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PREFACE 



Part I of the Guide to Writing OS/32 Driver's Manual is a tutorial for writing basic drivers, with 
the last chapter devoted to more advanced concepts. Chapter 1 is a review of basic terminology and 
concepts. Chapter 2 covers the essentials for writing driver code and Chapter 3 gives complete 
information for including a driver in the operating system. Two sample drivers are provided in 
Chapter 4, a simple digital input/output (DIO) interface and a complex TELEX tridensity magnetic 
tape driver. Chapter 5 introduces advanced concepts in drivers. These include the translation table, 
nonphysical device drivers and supervisor call 6 (SVC6) and trap generating device drivers. 
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CHAPTER 1 



INTRODUCTION 



1.1 BASIC CONCEPTS 

When a new user installs Perkin-Elmer's OS/32, it is often necessary to connect the operating 
system to the user's equipment and peripherals via a customized driver. Figure 1-1 demonstrates 
this situation. 
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Figure 1-1. The Customized Driver as Interface 



The Perkin-Elmer input/output (I/O) driver performs I/O to the device at the hardware level, such 
that user programs merely issue reads and writes, thus making the command sequences for each 
type of device transparent to the user. FORTRAN and other high-level languages use READ and 
WRITE statements which are translated into supervisor call 1 (SVC1) instructions by their 
respective compilers. The operating system then executes the SVC1 which calls the device driver 
to do the I/O to the requested device. 
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How does the system get into the I/O driver? 
EXAMPLE: A FORTRAN program 

READ (1,900) IX 
is translated by the compiler into: 

SVC 1,PBLK (assembly code) 
which is then assembled into object code: 

E110 xxxx 

The El is the op code for an SVC which causes the OS to initiate the I/O. 

For those of you who are interested, the operating system processes the SVC instruction in 
module EXIN (set up in low memory to handle microcoded vectors from the SVC instruction). 
EXIN passes the I/O request (SVC1) to module EXIO which handles pre and postprocessing of 
the I/O. EXIO validates the request, dispatches the driver and processes I/O termination as in the 
following: 

EXIN >EXI0 >driver >EXI0 

1.2 TERMINOLOGY 

For the user who is unfamiliar with Perkin-Elmer terminology, those terms required for use of this 
manual are given here. The order in which these terms are presented correspond to the structural 
level within the software at which they are encountered. 

• User task (u-task): a complete applications job, typically written in a high-level language such as 
FORTRAN, COBOL and Pascal. A u-task can be written in Common Assembly Language/32 
(CAL/32), although the existence of powerful optimizing compilers greatly reduces the 
requirements for u-tasks written in CAL/32. A u-task performs a useful applications function. 

• SVC1: an SVC code 1 is a single machine-level instruction that can be issued by a u-task to 
initiate an I/O operation. All Series 3200 Processors provide this instruction. Typically, 
the SVC1 instruction is issued by a user-callable subroutine or by code compiled as the result 
of high-level language statements being processed into machine code by a compiler. Typically, 
the user is not explicitly aware of the SVC1 instruction. The user simply issues reads and 
writes. 

• SVC1 parameter block: the SVC1 instruction references a six-fullword (24 byte) block which 
defines the I/O operation and is interpreted by the OS/32 I/O subsystem. The definition of 
the SVC1 parameter block does not necessarily concern the writer of a device driver. If 
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the driver performs device-dependent functions, then the SVC1 parameter block can be 
partially redefined by the device driver. 

• Device control block (DCB): This is the principle structure with which the writer of a device 
driver must be concerned. The DCB provides all of the parameters required to define the device 
to both the device driver and to the OS/32 I/O subsystem software. The DCB consists of a 
device-independent and a device-dependent segment. The device-independent segment is defined 
in the same manner for all devices. A device driver can reference data in this area, but in 
general can alter only a few specific items, since it is reserved for the OS/32 I/O subsystem. 
The device-dependent segment can be defined differently for each type of device and can be of 
arbitrary size. There is exactly one, and only one, DCB for each device configured in a 
system. For example, a system with four CRTs and a disk drive contains five DCBs. 

• Channel control block (CCB): This is a small control block defined by the interrupt service 
features implemented in the microcode of the Series 3200 Processors. An additional area of 
the CCB has been defined by OS/32 for use by device drivers. The CCB is the mechanism 
available to the device driver for passing control and device information to the interrupt 
service routines in the device driver. 

• Device driver: A software module consisting of both a definition of the DCB for a specific 
type of device, and various sections of executable code required to actually control the device, 
communicate with the OS/32 I/O subsystem, and service device interrupts in a manner 
consistent with the Series 3200 Processor interrupt service scheme. In addition to the DCB, a 
device driver written to control any interface consists of a CCB, a driver initialization 
routine (DIR), one or more interrupt service routines (ISRs) and one or more event service 
routines (ESRs). Several other routines, specified by the I/O handler list (IOH) are 
options. 

• Interrupt service pointer table (ISPT): An ordered list containing one entry for each possible 
device address in the system. This table starts at memory location X'DO' with each entry 
occupying one halfword. It is the responsibility of the software controlling the I/O (the device 
driver) to set up this table with the address of the immediate ISR or the address of the CCB+1 
for auto driver channel operation. 

• Auto driver channel: A microcode routine which is entered whenever the halfword entry in the 
ISPT is odd. This routine interprets the address in the ISPT as the address of a CCB plus one. 
The CCB consists of a description of the operation to be performed, and a list of parameters 
associated with the operation. 

1.3 COMPONENTS OF A DEVICE DRIVER 

A device driver is divided into major components that carry out all necessary functions. The most 
important functions are described in the following list. 



48-190 F00 R00 1-3 



• Driver initialization routine (DIR): 

The DIR is the first section of code executed in a device driver. Generally, it performs 
certain bookkeeping functions and the initial communication to the device hardware 
interface to set up the I/O operation. The I/O subsystem uses register set 5 for driver 
initialization service. The user does not have to worry about saving and restoring registers 
upon entry and exit from driver initialization routines. The writer of an I/O driver can 
use 15 of the 16 registers of set 5. Register D, which contains the DCB address, must not be 
destroyed. Routines in EXIO require that this register contain the DCB address after exit 
from the driver. 

• Interrupt service routine (ISR): 

ISRs service the hardware interrupts from the device interface. Generally, the ISR performs 
the minimum amount of control required to maintain the progress of the I/O operation and to 
determine when the operation is complete. When coding an ISR, certain register conventions 
must be upheld to insure the integrity of the system. The operating system expects registers 
8-F of set to be untouched by the driver. Therefore, the writer of an ISR should use only 
registers 0-7 of set 0. The register set selected (0,1,2, or 3) depends upon the hardware 
configuration. Normally, this would be set 0. If other than 0, in addition to backplane 
wiring, Sysgen32 or cupmt must also reflect the interrupt level in the device specifications. 

NOTE 

If set 1, 2, or 3 is used, of course, all registers would be 
available for ISR use; however, for compatibility, it is 
strongly suggested that only 0-7 be used. 

When an ISR is entered, the microcode sets the program status word (PSW) to X'2800', which 
enables all higher level interrupts and machine malfunction interrupts. If it is necessary to start 
two or more devices at the same time, it is usually necessary to disable all interrupts if your 
interrupt level is 1, 2 or 3. This prevents higher level interrupts from disrupting the appropriate 
sequencing of operations. The PSW to disable all interrupts, leaving machine malfunction 
enabled is X'2000*. 

• Event service routine (ESR): 

ESRs provide termination functions, such as shutting down the device, issuing retries where 
appropriate and doing various bookkeeping functions for the OS/32 I/O subsystem . 

. The I/O handler (IOH): 

An IOH is an ordered parameter list which defines the appropriate processing routines for 
various I/O functions. The list is defined by the $IOH macro. Special routines for 
initialization, end of task, as well as device-dependent functions can be defined via an IOH. 
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These IOH routines are called by various modules within the operating system. EXIO checks 
for read, write and command function IOH entries. EXIN checks for the presence of an 
initialization IOH during the SYSINIT routine. If an INIT IOH has been specified, EXIN does 
a branch and link to the routine. EXSV, during end of task processing, checks for the presence 
of an EOT IOH. If this routine exists, EXSV does a branch and link to the routine. 



The following is a sample of the way the IOH macro is used within a device driver. Since 
this is a macro, column 72 must contain a continuation character, and each item except the last 
is followed by a comma. 



IOH NAME=MMDIOH, 
READ=BARERD / 
WRITE=BAREWR, 
AIT=SVC1WAIT, 
TEST=SVC1TEST / 
SET=BARERD, 
HALT=SVC1N00P , 
REW=SVC1N00P, 
BSR=SVC1N00P, 
FSR=SVC1N00P, 
FFM=SVC1N00P / 
BFM=SVC1N00P , 
INIT=INIT.MMD / 
WFM=SVC1N00P 



1 
1 
1 
1 
1 
1 
1 
1 
1 
1 
1 
1 
1 



Some of the entries in the IOH list are as follows: 



INIT: 



If a device requires some special setup at system initialization time, the INIT parameter can be 
used to specify the name of the routine to be executed. The sysinit code in EXIN branches 
and links to this routine. An example of such processing would be the initialization of a 
driver's internal table. 

Register Conventions: 



Entry: 



Exit! 



R8 return address 

Rll DCB address 



R8 return address 

Rll DCB address 

All other registers can be 
destroyed. 
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EOT: 

If a driver must perform special cleanup operations when a task terminates, then the EOT 
parameter must be specified. At EOT time, the SVC3 process or (module EXSV) checks for 
an EOT handler for each logical unit (lu). The drawback to this cleanup method is that if the 
logical units are already closed, then no cleanup is done, since there is no close IOH. 

Register Conventions : 



Entry: 



Exit: 



R8 return address 

R9 .TCB of task going 

to end of task 

RIO DCB address 



R8 return address 

R9 TCB of task going 

to end of task 

RIO DCB address 

All other register can be 
destroyed. 



. DDF: 



A device-dependent function is a routine that is to be executed for a particular device. The 
function code for all device-dependent functions is X'81'; however, each device driver 
defines this code in a manner specific to each device. See Chapter 4 for more 
information on mag tape drivers. 

1.4 OS/32 DRIVER INTERFACE ROUTINES 

The writer of an I/O driver needs only to know when and how to call OS/32 routines. There 
is no need to be intimately familiar with the details of the operating system interface routines. 

DIRDONE - a routine called at the end of a DIR. This routine sets DCB.ESR with a default 
termination handler. (Register D must contain the address of the DCB.) 



B 



DIRDONE 



IODONE - a routine called at the end of ESR. This routine places the status in the SVC1 
parameter block (if any), sets a requested task trap, removes the task from an I/O wait and 
disconnects the leaf from the tree. (Register D must contain the address of the DCB.) 



B 



IODONE 



EVRTE - a routine which is called after a driver has modified the address of the termination 
routine. This routine is called in place of DIRDONE. (Register D must contain the address of 
the DCB.) 



B 



EVRTE 
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EVMOD - a routine in module EXIO to set another entry as the ESR address (modifies 
DCB.ESR). For current revisions of the operating system, some system overhead can be 
eliminated by performing this function directly: 

LA UE , TERMXXX1 

01 UE,Y' 80000000' set Indicator like EVMOD does 

ST UE,DCB.ESR(UD) 

In most cases, it is recommended that this subroutine convention be used, so that the 
driver is compatible with future revisions of OS/32. (Register D must contain the address of the 
DCB.) 

LA UE,TERMXXX1 set new term address 
BAL U8, EVMOD 

EVREL - a routine to release resources such as controllers and selector channels (SELCHs) 
acquired by a driver. 

LIS UE,3 release at SELCH level 

L UF , DCB. LEAF (UD) 
BAL U8 , EVREL 

TOCHON - a timer routine that is called, usually before a SINT instruction, to enable the system 
to return a time-out condition if a device does not respond within a given period of time. 
(Register D must contain the address of the DCB.) 

BAL U8 , TOCHON 

TOCHOFF - a timer routine that is called, after the driver has finished its work, to remove a 
given device from the time-out chain. (Register D must contain the address of the DCB.) 

BAL U8,T0CH0FF 

III - an entry point in module EXTI. This routine is the null interrupt routine which performs an 
LPSWR. The address of III is stored in the ISPT when the system is to perform no action upon a 
device interrupt. 

LA E7,III 

STH E7,ISPTAB(E2,E2) 

SQ - the address of the system queue. This structure is used by a driver ISR to schedule driver 
termination. 

L E6, DCB. LEAF (E5) 

ATL E6,SQ 

The above routines are the major interfaces between a device driver and OS/32. 
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Associated subroutine file: SUBS.MAC - contains commonly used subroutines for driver use. 
For efficiency, since many of these routines are only one or two lines of code, it is recommended 
that the code be placed in-line (especially for interrupt service coding). 

1.5 DRIVER COMMUNICATION WITH THE TOTAL COMPUTER SYSTEM 

The DCB is the principle means by which a device driver communicates with the rest if the system. 
Most of the DCB fields are used by various other components of the system to define the 
environment or a specific operation to the driver; a few DCB fields are used by the driver to report 
the results of an operation to the remainder of the system. In certain situations, specific registers 
are used to communicate between the driver and the operating system or processor firmware. 

The following system components communicate with a device driver: 

1. The user, who issues an SVC1 instruction. 

2. The operating system, which provides several services. 

3. The user, who defines the system through system generation (sysgen) parameters. 

4. The sysgen process, which allocates data structure areas. 

5. The processor firmware, which responds to interrupts. 

6. The writer of the driver, who defines values in the DCB. 

The writer of a driver must be aware of how each one of these system components communicates 
with the device driver. 

The user of the system issues an SVC1 instruction to initiate an I/O operation. The associated SVC1 
parameter block defines the operation to be done and receives some information on the results of 
the operation. The communication between the user and the driver is carried out by the operating 
system. The situation is equivalent to two people carrying on a phone conversation: each person 
accesses his own telephone set; the telephone company's equipment moves the signals between the 
two telephone sets. 

The USER accesses The DRIVER accesses 

an SVC1 parameter the DCB fields: 

block: 

SVC1.FC I/O function code > DCB.FC 

SVC1.LU lu number > DCB.LU 

SVC1.STA < operation result status DCB. STAT 

SVC1.SAD I/O buffer start address > DCB.SADR 

SVC1.EAD I/O buffer end address > DCB.EADR 

SVC1.RAD "random address" > DCB. RAND 

SVC1.LXF < length of transfer DCB.LLXF 

SVC1.X0P (user -defined) > DCB.SV1X 



1-8 48-190 F00 R00 



In addition to moving operation parameters between the DCB and the user's SVC1 parameter block, 
the operating system is responsible for starting the execution of various sections of the driver, being 
sure that the driver does not take too much time to complete the operation and informing the driver 
as to which device the operation is to be directed to. 



The Operating 
System: 



The Driver : 



Register 13 



address of DCB 



•> Register 13 



DCB.ESR <- 



address of the 
next event service 
routine to execute 



DCB.ESR 



DCB. TOUT <• 



time-out value 



•> DCB. TOUT 



SQ < event tree leaf address - 

(schedules ESR execution) 



DCB . LEAF 



DCB . UPBK 



address of the 
user's SVC1 block 
as seen by the 
user 



-> DCB. UPBK 



DCB.PBLK 



address of the 
user's SVC1 block 
as seen by the 
driver 



-> DCB.PBLK 



DCB.TCB 



address of the 
task control block 
for the user 



•> DCB.TCB 



Note that since register 13 always points to the DCB, it is important that the driver never modify it. 
The DCB.TOUT field is used by all drivers. The DCB.ESR field is occasionally used. The fields 
DCB.UPBK, DCB.PBLK and DCB.TCB are almost never needed by a device driver. These fields 
are listed here only because a few special circumstances require them. 

The user (perhaps unknowingly) defines some parameters through the specifications written in a 
sysgen file. For example, the user writes the statement: 

D300: ,FE,54,SELCH=F0,C0NTR=FB 
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This is mapped to the DCB as follows: 

"FE" device address > DCB.DN 

"54" device type code > DCB.DCOD 

"SELCH=FO" --- SELCH address > DCB.SDN 

"CONTR=FB" controller address > DCB.CDN 

For another example, the user writes: 

MD5E : , 5E , 39, XDC=X0810, RECL=132 

This is mapped to the DCB as follows: 

"5E" device address > DCB.DN 

"39" device type code > DCB.DCOD 

"XDC=OC0810" --- user-defined -- ---> DCB.XDCD 

"RECL=132" device record length > DCB.RECL 

When the sysgen procedure is run, various data structure areas (such as the DCB) are assigned 
physical locations within the operating system. It is necessary that these data structures contain 
pointers to other data structures within the system, so that the various operating system routines can 
find their way around. For example, a device driver must be able to locate the DCB if it knows only 
the location of the CCB. The operating system must be able to locate the start of the device driver 
if it knows only the location of the DCB. Since these pointers are set up at sysgen time, they are 
static and must never be modified by the driver. Some of these pointers are: 

Sysgen procedure Driver 



DCB. CCB address of CCB > DCB. CCB 

CCB. DCB address of DCB > CCB. DCB 

DCB. LEAF event tree leaf address -> DCB. LEAF 



Some entries in the DCB are used primarily by the operating system to locate various routines 
within the driver. These fields are set up at sysgen time, and are not modified by the driver. These 
fields include: 



Sysgen procedure 



operating system 



DCB.INIT address of driver's > DCB.INIT 

initialization routine 

DCB. TERM . address of driver's > DCB. TERM 

termination routine 
address of driver's 

DCB.FUNC command function > DCB.FUNC 

processing routine 
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A device driver must also communicate directly with the processor firmware routines that process 
interrupts. The driver must tell the processor what ISR is to be executed to process the next 
interrupt from the device. The processor must in turn tell the ISR what device interrupted and 
where the associated CCB is located. Also, the processor provides the ISR with the proper PSW and 
location counter with which to exit from interrupt service. The communication between the 
processor and the driver is as follows: 

Processor hardware Device 

and firmware driver: 

ISPTAB < address of CCB DCB.CCB 

CCB.SUBA < address of ISR to execute -- "LA" instruction 

hardware -- address of interrupting device -> register 2 

hardware -- status of interrupting device --> register 3 

microcode address of CCB > register 4 

microcode PSW at time of interrupt > register 

microcode LOC at time of interrupt > register 1 

1.8 A SPECIAL NOTE ON DEVICE TIME-OUTS 

OS/32 uses the line frequency clock (LFC) (which interrupts 120 times per second) to maintain 
the device time-out mechanism. Every second, the system decrements the time-out constant for 
each device by one. If the time-out constant is X'TFFF', the device cannot be timed out. 
When a driver's interrupt service has gone to completion, the time-out constant should be set to -1 
(X'FFFF') to indicate that a time-out did not occur. If the time-out constant decrements to zero, 
the device did not respond in the specified length of time and the driver should set an X'8282' 
status, to indicate time-out. 

The timer management routine which controls the device time-out mechanism is the OS/32 module 
EXTI in routine TIMCH3. If this routine finds X*7FFF\ 0, or a negative value in DCB.TOUT, it 
processes the next device on the time-out chain. The value in DCB.TOUT is decremented by one 
and if the value is now zero, the device has timed out. If this time-out condition occurs, EXTI adds 
the device leaf to the system queue for termination processing. 

Drivers should always check for time-out before adding a leaf to the system queue. Crash code 153 
may result if a leaf is added to the system queue twice. A safety check mechanism in EXIO 
prevents the item from being added twice (if the system is generated with safety checks enabled). 
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CHAPTER 2 
WRITING THE DRIVER 



2.1 INTRODUCTION 

The previous chapter outlined the basic components required to write a device driver. These basic 
components included the device control block (DCB) relationships, the input/output (I/O) 
subsystems relationships and the specific routines required within the device driver. With this 
conceptual background, the user can now address the essential question, "How do I write the code?" 

2.2 WRITING DRIVER CODE 

The best way to begin a discussion of writing driver code is to begin with an anyalysis of some 
simple examples. The following examples show very basic drivers. 

Step 1: The Simplest Case 

The following is the simplest possible routine that satisfies the basic operating system interface 
requirement for a driver. This driver performs only the function of branching back to the operating 
system. The termination routine is never executed, since the initialization routine branches to the 
I/O operation complete routine in the operating system. 

The last instruction executed by a driver must be a branch to IODONE, which is an entry point to 
the operating system. This is the only way that a driver can indicate to the operating system that the 
I/O operation is complete. The operating system enters the driver at the label INITDVR1. This 
label is specified in the DCB. Standard Perkin-Elmer convention requires that the first four 
characters be INIT. 

* 

INITDVR1 B IODONE branches back to the operating system 

* 

TERMDRV1 EQU * this will never be executed 

* but must be here because it must 

* be specified in the DCB. 
END 

Step 2: Scheduling Event Service Routine (ESR) 

To schedule an ESR routine, add the contents of the DCB. LEAF field to the system queue. This 
can be done anywhere in the driver, but normally is done only in an interrupt service routine (ISR), 
as is illustrated later. Since this driver only has one ESR routine, (the termination routine), this is 
the ESR scheduled, by default. 
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This driver also illustrates another basic operating system interface, which is the branch to 
DIRDONE. A driver which has initiated an I/O operation, but has not completed that operation, 
should branch to DIRDONE (another entry in the operating system) to allow the processor to do 
other unrelated tasks while the I/O operation is in progress. Branching to DIRDONE normally 
forces the next ESR routine that is executed to be the termination routine, labeled TERM..., as 
specified in the DCB definition. 

This driver also illustrates the fact that register 13 (UD) always points to the DCB of the device to 
which the I/O is directed. The operating system sets up this register before branching to the driver. 
The contents of register 13 should never be modified by the driver, for several reasons that will be 
shown more completely later. 

* 

* SCHEDULE ESR EXECUTION THROUGH SYSTEM QUEUE SERVICE 



INITDRV2 L 

ATL 

B 
* 
* 

TERMDRV2 B 
* 

END 

* 



UO, DCB. LEAF (UD) 

UO,SQ 

DIRDONE 



IODONE 



Driver is always entered 
with reg 13 = addr of DCB 
Register set 5 is always 
used, except on some 
8/32 and all 7/32 CPUs. 



Step 3: Setting Up Entry To ISRs 

The following example illustrates the basic execution sequence of a typical driver: from initialization 
to interrupt service to termination. This driver utilizes the minimum possible code to set up a path 
for entry to an ISR. It also illustrates the important step of entering an ISR to initiate an I/O 
operation. This is done to avoid responding to an unexpected interrupt while the device is being 
started. Also, as will be shown later, it is sometimes necessary to insure that certain sequences of 
operations are executed without any interruption, due to timing requirements. This can only be 
accomplished in an ISR. 

In this driver, the initialization routine consists only of the code required to set up the interrupt 
service routine. The termination routine consists only of the exit to the operating system. The one 
ISR is entered by execution of the SINT instruction, since it is the first ISR to be executed. Since it 
is also the last ISR to be executed, it dismantles the path to itself, to avoid responding to any 
additional interrupts from the device. 



2-2 
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INITDRV3 EQU * entry point specified by DCB 

LH U2,DCB.DN(UD) get physical address of device 

LHL UCDCB.CCB(UD) get address of CCB for device 

LIS U0,0 set up a nonexecute command 

STH UO,CCB.CCW(UC) into the channel control word 

LA UO,ISRO put the address of the 

STH UO,CCB.SUBA(UC) ISR into the CCB 

AIS UC,1 make CCB address odd for ISPT 

STH UCX'DO' (U2,U2) put CCB addr into ISPT 

LH U1,DCB.ILVL(UD) get the interrupt level 

SI NT U1,0(U2) force entry into the ISR 

* 

* (the code at "ISRO" is now executed; after the 

* ISR exits, the following instruction is executed) 



* 



B DIRDONE after exit from first ISR, 

go back to the OS. 



* The following ESR is executed sometime after 

* the branch to DIRDONE is executed. It is executed 

* because it was scheduled by the ISR routine. 
* 

TERMDRV4 EQU * termination routine entry 

B IODONE exits to operating system 

* 

* The following ISR is entered 

* by execution of the SINT instruction. The ISR is in 

* "PURE" code to insure that it is located 

* in the lower part of memory (it must be in the first 

* 64KB of memory) . The ISR schedules the ESR for 

* execution, and disables further interrupts. 
* 

* Note that on entry to the ISR, the following registers 

* have been set up by the processor microcode: 
* 

* E0,E1 = return program status word (PSW) /location counter (LOC) 

* E2 = address of interrupting device 

* E3 = status of interrupting device 

* E4 = address of CCB for interrupting device 

* 
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ISRO 



EQU 


* 


L 


E5,CCB.DCB(E4) 


LA 


E7,III 


STH 


E7,X'DO' (E2,E2) 


L 


E6,DCB.LEAF(E5) 


ATL 


E6,SQ 


LPSWR 


EO 



get address of associated 

DCB out of CCB. 

put address of null 

interrupt return into ISPT 

now schedule the ESR for 

execution. 

exit interrupt service 



NOTE 



The examples in Steps 1, 2, and 3 are all complete 
drivers with respect to the operating system. The reader 
can include any one of them into a system; an 
supervisor call 1 (SVC1) directed at a "device" handled 
by one of these drivers always returns immediately to 
the caller. Any one of these three drivers can be used to 
time basic SVC1 service processor overhead. 

Step 4: Executing a Sequence of ISR 

In the example in Step 3, there was only one ISR, which is generally not very useful. To control a 
real device, we must have a minimum of two ISR routines: one to start the device and one to stop 
the device. The initialization routine sets up the interrupt path to the first ISR; the first ISR sets up 
the interrupt path to the second ISR and starts the device. The second ISR receives the hardware 
interrupt, stops the device, dismantles the interrupt path and schedules the ESR for execution; the 
ESR exits to the operating system. 

For ease of understanding the sequence of execution of code, the following driver is written in a 
way such that the lines of code are in the same order as they are executed by the processor. This is 
an acceptable way to write a driver, as long as the placement of the IMPUR and PURE statements 
is correctly done. 

However, the reader will probably find that a listing of the driver with the code organized as shown 
in the example for Step 3 is easier to use when debugging on a system, as all of the IMPUR and 
PURE code listings are separated into two separate blocks, just as it is in memory. 
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IMPUR 




INITDRV4 


EQU 


* 




LH 


U2,DCB.DN(UD) 




LHL 


UC,DCB.CCB(UD) 




LIS 


UO,0 




STH 


UO,CCB.CCW(UC) 




LA 


UO,ISRO 




STH 


UO,CCB.SUBA(UC) 




AIS 


UC,1 




STH 


UCX'DO' (U2,U2) 




LH 


U1,DCB.ILVL(UD) 


* 


SINT 
PURE 


U1,0(U2) 


ISRO 


EQU 


* 




LA 


E7,ISR1 




STH 


E7,CCB.SUBA(E4) 



entry point from operating system 

get physical address of device 

get address of CCB for device 

set up a nonexecute command 

into the channel control word 

put the address of the 

ISR into the CCB 

make CCB address odd for ISPT 

put CCB addr into ISPT 

get the interrupt level 

force entry into the ISR 



entered from SINT instruction 

get address of next ISR 

& put into CCB to set up path 



* 
* 

* 

* 

* 
* 

A 
* 

* 

* 

I SRI 
* 



(commands to start the device go here) 



LPSWR EO 



IMPUR 



exit from this ISR 
(returns to instruction after 
SINT, which is as follows: 



Now exit to the operating system to let the CPU do some unrelated 
activity while we wait for the hardware interrupt: 



B 



EQU 



LA 
STH 



DIRDONE 



E7,III 
E7,ISPTAB(E2,E2) 



this is logically part of 
the initialization routine 

The interrupt from the 
hardware will force this to 
be executed . 

get address of null interrupt 
routine & put into ISPT to 
disable receipt of more Int's. 



(commands to stop the device go here) 
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L E5,CCB.DCB(E4) 
L E7 , DCB. LEAF (E5) 
ATL E7,SQ 
LPSWR EO 



get address of DCB for device 
get value to put on SQ to 
schedule ESR execution 
exit this ISR. 



IMPUR 
TERMDRV4 EQU * 

B IODONE 



termination routine 

exits to operating system. 



Step 5: Setting Up Device Time-outs and User Status 

The operating system is used to force an ESR to be executed if the I/O operation takes too much 
time. This happens if the device somehow does not work right. The code sequence shown below is 
used to tell the operating system to force a "time-out" (which means forcing an ESR to be executed) 
if the operation does not complete within a the number of seconds specified by the driver. 

A time-out should always be set up before starting an I/O operation. The reason for doing this is 
that if the device should ever fail to interrupt, the I/O operation would not complete. This in turn 
would cause the user task (u-task) that issued the I/O operation to be "stuck": it could not be 
removed from the system (cancelled). 

This sample driver illustrates the proper interface to the operating system for "getting on and off the 
timer chain": in other words, specifying the time-out interval, and how to tell the operating system 
to start and stop timing the I/O operation. Notice that the value DCB.TOUT must be set and reset 
in an ISR to avoid a possible conflict with the operating system routines that are necessary for the 
timing of the I/O operation. 



IMPUR 
INITDRV5 EQU 



entry point from operating system 



BAL U8,T0CH0N 



LH 


U2,DCB.DN(UD) 


LHL 


UCDCB.CCB(UD) 


LIS 


U0,0 


STH 


UO,CCB.CCW(UC) 


LA 


UO,ISRO 


STH 


UO,CCB.SUBA(UC) 


AIS 


UC,1 



this call tells the operating system 
to be ready to time an I/O operation 
This call MUST be made in either 
the initialization routine or 
an ESR routine, NEVER in an ISR! 
This call leaves DCB . TOUT= * 7FFF ' 

get physical address of device 

get address of CCB for device 

set up a nonexecute command 

into the channel control word 

put the address of the 

ISR into the CCB 

make CCB address odd for ISPT 
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put CCB addr into ISPT 
get the interrupt level 
force entry into the ISR 



ISRO EQU * entered from SINT instruction 

get address of next ISR 
& put into CCB to set up path 
get address of DCB 

* 

* now "turn on" the timing of the operation by the operating system: 



STH 


UCX'DO' (U2,U2) 


LH 


U1,DCB.ILVL(UD) 


SINT 


U1,0(U2) 


PURE 




EQU 


* 


LA 


E7,ISR1 


STH 


E7 / CCB.SUBA(E4) 


L 


E5,CCB.DCB(E4) 



* 



LIS E7,5 specify a five second time-out 

STH E7, DCB. TOUT (E5) by putting 5 into DCB. TOUT 

(notice: it is a HALFWORD!) 



* (commands to start the device go here) 

* 

LPSWR EO exit from this ISR 

* 

IMPUR 

B DIRDONE this is logically part of 

* the initialization routine 
* 

* Since a value of 5 was set into DCB. TOUT, no more than 

* five seconds can elapse before the hardware interrupts. 

* If the interrupt does not occur, the driver is 

* reentered by the operating system at ' TERMDRV5 * , and 

* the code at 'I SRI' is not executed. 
* 

I SRI EQU * The interrupt from the 

* hardware forces this to 

* be executed. 

LA E7,III get address of null interrupt 

STH E7, ISPTAB(E2,E2) routine & put into ISPT to 

* disable receipt of more int's. 
* 

* (commands to stop the device go here) 



* 



E5 / CCB.DCB(E4) get address of DCB for device 
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* Now check that the operating system did not time-out the 

* operation just prior to the hardware interrupt occurring, 

* but before the ESR could dismantle the interrupt path. 

* This is a unlikely event, but must be checked for the 

* possibility. If the operating system times out the operation, 

* DCB.TOUT = 0, and the execution of the ESR is already 

* scheduled. Therefore, if the ISR finds that DCB.TOUT = 0, 

* then the ISR should not try to schedule the ESR. Doing so 

* can cause a system crash under some software configurations. 



* 

LH E7, DCB.TOUT (E5) get current DCB value 

BZ ISR1EXIT if already zero, exit now. 

* 

* Since some time elapses between now and the time that 

* the ESR is executed, it is necessary to indicate to both 

* the operating system and the ESR that the operation 

* completed (i.e., the expected interrupt was received vrithin 

* the specified length of time) . The operating system expects 

* that the value 'FFFF' is used for this purpose. 
* 

LCS E7,l get value of 'FFFF* 

STH E7, DCB.TOUT (E5) to set in DCB.TOUT 
L E7, DCB. LEAF (E5) get value to put on SQ to 
ATL E7,SQ schedule ESR execution 

* 

ISR1EXIT LPSWR EO exit this ISR. 

* 

* The termination routine customarily sets a status for the 

* user of '8282' if a time-out has occurred; otherwise some 

* other status is set, such as '0000' if the operation completes 

* normally. Thus, the termination routine checks the time-out 

* value to determine what has happened. The value put into 

* into DCB. STAT is copied by the operating system into the 

* user's SVC1 parameter block, so that the user can know 

* of the success or failure of the requested operation. 
* 

IMPUR 

termination routine 
get the time-out value 
if zero, we timed out 
and set zero user status 



IMPUR 




TERMDRV5 EQU 


* 


LH 


Ul, DCB. TOUT (UD) 


BZ 


TIME0UT5 


LIS 


U2,0 


STH 


U2, DCB. STAT (UD) 
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TERM5X 



EQU 
BAL 



B 



U8,T0CH0FF 



IODONE 



now tell operating system 
that we do not need any more 
timing services 

exit to operating system. 



TIME0UT5 LHI U2,X'8282' on time-out, tell user what 
STH U2 , DCB . STAT (UD) happened . 
B TERM5X go to common processing 

Step 6: Selector Channel (SELCH) I/O, Data Buffer Addresses, and Length of Transfer 

NOTE 

If your custom device operates under direct processor 
control on the processor multiplexor bus, you may wish 
to skip directly to Step 7. 

Many custom devices operate under a SELCH. To control the I/O operation, both the custom 
interface and the SELCH must be controlled. The basic points to be considered when a SELCH is 
used to control a device are: 

1. The SELCH must have the starting and ending addresses of the data buffer in memory written 
to it before the transfer starts. 

2. Once the SELCH is commanded to start the transfer, the device under the SELCH cannot be 
addressed. The SELCH must be stopped before the device can be accessed. 

3. The SELCH terminates the transfer, and interrupts the processor, when either of two 
conditions are met: 

a. The SELCH determines that the data transfer has proceeded to the end of the data 
buffer; in other words, either all of the data in the user's buffer has been sent to the 
device, or the user's buffer has been filled with data from the device. 

b. The device controller indicates to the SELCH that no further data transfer is possible, by 
activating the appropriate signals on. the SELCH private bus. (How this happens 
electrically is of no importance to the driver software). 

The following driver, which is complete except for the specific commands required to control the 
device, shows all of the steps required to control an I/O operation through a SELCH. To aid 
comprehension, all of the SELCH commands are explicitly written. In many Perkin-Elmer supplied 
device drivers, subroutines are called to interface to the SELCH. Those routines perform the same 
functions as the code written here. It is a matter of individual programming preference as to 
whether those subroutines are used, or the commands are written explicitly as shown here. The 
routines used by some Perkin-Elmer drivers can be found in the module SUBS.MAC; if you plan to 
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use these subroutines, you should refer to the source code in this module to determine the proper 
calling sequences. 

The fields DCB.FC, DCB.SADR, DCB.EADR, and DCB.LLXF are used in this driver to control 
the SELCH. The driver references, but does not modify, DCB.FC, DCB.SADR and DCB.EADR. 
The driver does set DCB.LLXF, which is then copied by the operating system back into the user's 
SVC1 parameter block to allow the user to know how much data was actually transferred. The field 
DCB.FC, which is copied directly from the user's SVC1 parameter block, is used to determine 
whether to set the SELCH and the device in a device read or device write mode. 





IMPUR 




INITDRV6 EQU 


* 




BAL 


U8,T0CH0N 




LH 


U3,DCB.SDN(UD) 




LHL 


UCDCB.CCB(UD) 




LIS 


U0,0 




STH 


UO,CCB.CCW(UC) 




LA 


UO,ISRO 




STH 


UO,CCB.SUBA(UC) 




AIS 


UC,1 


* 


STH 


UC,ISPTAB(U3,U3) 




LH 


U1,DCB.ILVL(UD) 


* 


SINT 
PURE 


U1,0(U2) 


ISRO 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LA 


E7,ISR1 




STH 


E7,CCB.SUBA(E4) 




LH 


E3,DCB.SDN(E5) 




OC 


E3,SLCHST0P 



entry from operating system to start I/O 

go get on timer chain 

get address of the SELCH 

get address of CCB for device 

set up a nonexecute command 

* in the channel control word 
get the address of the first ISR, 

& set up for start-up SINT instruction 
make CCB address odd, for 

* set up of ISP table 
(note SELCH address is used) 
get the interrupt level 
force entry to first ISR 



entry from SINT to start I/O 

get address of DCB for device 

get address of next ISR 

& set up CCB for hardware interrupt 

get SELCH address 

be sure SELCH is reset 



* The values DCB.SADR and DCB.EADR were set up by the operating system 

* by copying the values SVC1.SAD and SVC1.EAD from the user's SVC 1 block, 

* and converting those values to physical memory addresses. 
* 

WD E3,DCB.SADR+1 (E5) write 24-bit starting addr 

WH E3,DCB.SADR+2(E5) * to the SELCH 

WD E3,DCB.EADR+1(E5) write 24-bit ending address 

WH E3 / DCB.EADR+2(E5) * to the SELCH 

LIS E6,5 set up the device time-out 

STH E6, DCB. TOUT (E5) value for the operating system 
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* Here are some things to consider at this point relative 

* to programming a SELCH-controlled I/O operation: 

1. Once the SELCH is commanded to a "go" state, the device is 
unaccessable from the processor. Thus, we must issue the 
appropriate commands to the device first, then start SELCH 

2. Some devices (e.g., magnetic tapes and disks), require that 
the SELCH be started at essentially the same instant as the 
device, to insure that a data overflow/underflow does not occur. 
Thus, ALL interrupts must be shut off while the device and 
SELCH are started! 

3. The SELCH (and typically the device) have different command 
sequences that must be used to start read and write modes . 
This driver uses two separate sets of code for starting read 
and write, to simplify understanding of the logic used. 

4. Most simple devices that operate under a SELCH are most efficiently 
programmed in such a way that only the interrrupt from the SELCH 
is needed toindicate the end of the transfer. Thus, the interrupts 
from the device may be left shut off or ignored, as is done in 
this driver. 



EPSR E7,E7 

NI E7,Y'FF20F0' 





LB 


E6,DCB.FC(E5) 




THI 


E6,X'40' 


* 


BNZ 


ISROR 


* 
ISROW 


EQU 


* 




EPSR 


E6,E7 




oc 


E2,DEVCWRIT 




oc 


E 3, SLCHWRIT 


* 


LPSWR 


EO 


ISROR 


EQU 


* 




EPSR 


E6,E7 




oc 


E2,DEVCREAD 




OC 


E3,SLCHREAD 




LPSWR 


EO 


SLCHSTOP 


DB 


X'48 1 


SLCHWRIT 


DB 


X'50* 



get current PSW value 
reset bit 20 for 
noninterruptable state 

get the function code that was 
specified by the user, then 
test for read/write, and go 
to the appropriate routine 

come here to start write I/O 
become noninterruptable 
start the device in write mode 
start the SELCH in write mode 
exit the ISR routine 

come here to start read I/O 

become noninterruptable 

start the device in read mode 

start the SELCH in read mode 

exit the ISR routine 

command to "stop" (reset) SELCH 

SELCH "go & write" command 
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SLCHREAD 


DB 


X'70' 


DEVCWRIT 


DB 




DEVCREAD 
* 


DB 
IMPUR 






B 


DIRDONE 



PURE 
ALIGN 2 



SELCH "go & read" command 
appropriate device write command 
appropriate device read command 



driver initialization routine 
exit back to operating system. 



be sure we are not on a 

byte boundary due to DB entries 

in previous ISR routine 



SELCH interrupt forces this 
routine to be executed. 



I SRI EQU * 

* 

* note that E2 contains the address of the SELCH 





OC 


E2,SLCHST0P 




LA 


E7,III 




STH 


E7,ISPTAB(E2,E2) 




L 


E5,CCB.DCB(E4) 




LH 


E6 / DCB.T0UT(E5) 




BZ 


ISRIX 




LCS 


E6,l 




STH 


E6,DCB.T0UT(E5) 




L 


E7,DCB.LEAF(E5) 




ATL 


SQ,E7 


ISRIX 
* 


LPSWR 
IMPUR 


EO 


TERMDRV6 

* 


EQU 


* 


* 


LH 


U3,DCB.SDN(UD) 


* 


OC 


U3,SLCHST0P 




RDR 


U3,U0 




RHR 


U3,U1 




SLL 


U0,16 




OR 


U0,U1 




C 


UO,DCB.EADR(UD) 




BNE 


TERM6X 



give the SELCH a stop command 
dismantle the interrupt path 

* to avoid any more interrupts, 
get address of DCB of device 
chech the time-out constant 

if already timed-out, do nothing, 
otherwise, indicate no time-out 
by setting flag to 'FFFF' 
now schedule the ESR to 

* be executed . 
exit from this ISR. 



operating system enters here 
for I/O operation termination 

get SELCH address 

be sure SELCH is stopped 

(if we timed-out, it may not be) 
now get SELCH final address 

(all 24 bits) 

make up a 24-bit value... 
now UO contains SELCH final addr 
is final addr = user's end addr? 
if not, branch to special logic 
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TERM6A 


S 


UO,DCB.SADR(UD) 




AIS 


U0,1 




ST 


UO,DCB.LLXF (UD) 




LIS 


U1,0 


TERM6B 

* 


STH 


U1,DCB.STAT(UD) 




BAL 


U8 , TOCHOFF 




B 


IODONE 



now calculate the length of xfer 
adjust for inclusive addressing 
and save length of xfer for user 
no error if equal, so set status 
for user . 

get off the timer chain 

and exit to operating system I/O termination. 



* The following code is executed only if there is not a final address match: 

* SELCH end address equals user's specified end address. Exactly what 

* should be done under these circumstances depends upon the device, and 



how the system designer wants it to behave. For the purpose of this 
driver, make the following choices: 

1. If the final address is not in the range of the 
the user's start and end addresses, then set the 
status = X'8490', the length of transfer to zero, 

and exit. (Some Perkin-Elmer supplied drivers crash the system 
deliberately if the final address is outside the 
user's start/end address, under some conditions.) 

2. If the operation timed-out, set the status = X'8282', 
set the length of transfer to zero, and exit 

3. If the operation did not time-out, but the end address 
is less than the user's end address, calculate the 
actual length of transfer, and set the status = 0. 



TERM6X 
* 



EQU 

C 

BM 

C 

BP 

LH 

BNZ 



U0,DCB.SADR(UD) 

TERM6E 

U0,DCB.EADR(UD) 

TERM6E 

U4,DCB.T0UT(UD) 

TERM6A 



come here if SELCH end addr 

is not equal user's end address 

check end address for being 

out of range 

* 

* 

did we time-out? 

if not, no error 



LHI Ul, X'8282' If time-out, set proper status 

LA U8,III and reset the ISP table 

STH U8,ISPTAB(U3,U3) * 

B TERM6B * 



TERM6E 



LHI 
B 



Ul, X'8490' 

TERM6B 



if end address out of range, 
set appropriate status 
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Step 7: Data Transfer Using Autodriver Channel Programming 

Many low-speed devices, primarily interactive terminals and some communications equipment, have 
controllers that are designed to present an interrupt to the processor for each character transferred. 
The following driver provides an explanation of the specific coding sequences that are peculiar to 
autodriver channel programming. 

Note that this driver is designed to operate on a byte transfer device. This means that: 

1. The device controller, when addressed, leaves the HWO (halfword) signal on the multiplexor 
(MUX) bus in the inactive (high) state. 

2. The device controller, in response to an active DRO signal on the MUX bus (i.e., data 
request), activates only eight data lines (D080 through D150). 

3. The device controller, in response to an active DAO sighal on the MUX bus (i.e., data 
available), responds to only eight data lines (D080 through D150). 

It is important to note that the distinction between byte- and halfword-oriented devices is made 
based on the behavior of the device controller on the MUX bus (or private SELCH bus). The 
characteristics of the data lines that the device controller present to the device have no bearing on 
the byte vs. halfword distinction for the purposes of autodriver channel programming. The 
hardware design manual, or circuit logic diagrams, for the device controller must be consulted to 
determine if the device controller is a byte or halfword device. 

INITDRV7 PROG Sample driver #7. 

NLIST 

$REGS$ 

$DCB$ 

$CCB 

LIST 

EXTRN DIRDONE , I I I , I ODONE , ISPTAB , SQ , TOCHOFF , TOCHON 

ENTRY INITDRV7,TERMDRV7 

IMPUR 
INITDRV7 EQU * entered here by operating system to do I/O op 

LH U2,DCB.DN(UD) get the device address 

LHL UCDCB.CCB(UD) get the address of the CCB 
* 

* For the purposes of showing how the two-buffer concept can be 

* used in autodriver channel programming, this driver outputs 

* a prefix and a suffix for each message the user writes to 

* the device. Thus, both buffer and buffer 1 are used. 

* 

* We initially set up buffer to output the prefix and buffer 1 to output 

* the user's message. Reuse buffer to output the suffix of the message. 
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* Since, by design choice, we wish for the complete line 

* of output to fit on the CRT screen, we will limit the 

* user to a message of 40 characters or less. If the user 

* specifies a message greater than 40 characters, the 

* initialization routine outputs a status of X'8490' 

* and a length of transfer of zero, and exit. This 

* illustrates the common practice of doing some initial 

* parameter and device status checks in the initialization 

* routine, before the first ISR is entered. 
* 

get the user ' s ending address 
& save as buffer 1 address, 
calculate requested message 

* length, then verify it is 
not greater than 40 . 
If more than 40, error exit, 
now calculate value to put 

* into CCB as buffer count 
& save for later use 

now set up the CCB for the 
prefix to be output 
(use buffer 0) 

calculate value for counter 
and save for later use. 

* At this point, both sets of buffer pointers are set up. 

* Set up the remainder of the CCB in the usual way to point 

* to the first ISR. Notice that we wait 

* until after the initial parameter checks to initialize the 

* I/O operation timing services of the operating system. We 

* do that now, and go to the first ISR. 
* 



L 


U0,DCB.EADR(UD) 


ST 


U0,CCB.EB1(UC) 


S 


U0,DCB.SADR(UD) 


AIS 


U0,1 


CHI 


U0,40 


BP 


INIT7ERR 


LIS 


Ul,l 


SR 


U1,U0 


STH 


U1,CCB.LB1(UC) 


LA 


Ul, PREFIX. S 


LA 


U0, PREFIX. E 


ST 


U0,CCB.EB0(UC) 


SR 


U1,U0 


STH 


Ul , CCB . LBO (UC) 



BAL 


U8, 


. T0CH0N 


LIS 


UO, 


,0 


STH 


uo, 


. CCB . CCW (UC) 


LA 


UO, 


. ISR0 


STH 


UO, 


CCB.SUBA(UC) 



go tell operating system we need timing done 

reset the channel command word 
* 

get' address of first ISR 
& save in CCB. 



* Use the CCB.MISC field to allow the ISR routines 

* to tell the ESR that a transfer failed, if this should 

* happen. Thus, we initialize this field to zero. 
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get a zero 

* 



LHI U0,0 

STH UO,CCB.MISC(UC) 

AIS UC,1 make CCB addr odd for ISPT 

STH UC,ISPTAB(U2,U2) (set up ISPT) 

LH U1,DCB.ILVL(UD) get the interrupt level 

SINT U1,0(U2) go start the transfer 

B DIRDONE after first ISR, exit to do 

something else while I/O runs 



initialization error exit 

get a status code 

& save for user . 

reset the length of transfer 

for user 

terminate the operation. 



come here to start transfer 
get address of next ISR to use 
and set up CCB for next ISR. 
get DCB address 
set up an 8 second time-out 
(this is an arbitrary choice) 
give the COMM-MUX command 2, 
& command 1 



The autodriver channel operates in response to interrupts . 

Since we are now in an ISR, we can not issue another SINT 

to start the I/O operation. Instead, we utilize the SCP 

instruction to maintain the buffer pointer /counter in the 

CCB, and do a WD to the device. This causes a hardware interrupt, 

which is then handled by the autodriver channel firmware. 



set the channel command word 

* for buffer 

get a character from buffer 

write it to the device 

and exit back to init routine 

execute, buffer 
execute, buffer 1 
COMM-MUX command 2 



* 






* 






INIT7ERR 


EQU 


* 




LHI 


U5,X'8490' 




STH 


U5, DCB. STAT (UD) 




LIS 


U0,0 




ST 


UO,DCB.LLXF(UD) 


* 


B 
PURE 


IODONE 


ISRO 


EQU 


* 




LA 


E7,ISR1 




STH 


E7,CCB.SUBA(E4) 




L 


E5,CCB.DCB(E4) 




LIS 


E6,8 




STH 


E6, DCB. TOUT (E5) 




OC 


E2,CMD2 




OC 


E2,CMD1 





LH 


E 6, CCWO 




STH 


E6,CCB.CCW(E4) 




SCP 


E7,CCB.CCW(E4) 




WDR 


E2,E7 




LPSWR 


EO 




ALIGN 


2 


CCWO 


DC 


X , A084' 


CCW1 


DC 


X'A08C 


CMD2 


DB 


X'F8' 
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CMD1 


DB 


X'63* 


DISARM 


DB 


X'CO' 


* 


ALIGN 


2 


I SRI 


EQU 


* 




LH 


E7,CCB.LB0(E4) 




BNP 


ISRERR 




LA 


E6,ISR2 




STH 


E6,CCB.SUBA(E4) 




LH 


E7,CCW1 




STH 


E7,CCB.CCW(E4) 




SCP 


E7 / CCB.CCW(E4) 




WDR 


E7,E2 


* 


LPSWR 


EO 


ISR2 


EQU 


* 




LH 


E7,CCB.LB1(E4) 




BNP 


ISRERR 




LA 


E6,ISR3 




STH 


E6,CCB.SUBA(E4) 




LA 


E7, SUFFIX. E 




ST 


E7 / CCB.EB0(E4) 




LA 


E6, SUFFIX. S 




SR 


E6,E7 




STH 


E6,CCB.LB0(E4) 




SCP 


E7 / CCB.CCW(E4) 




WDR 


E7,E2 


* 


LPSWR 


EO 


ISR3 


EQU 


* 




LH 


E6,CCB.LB0(E4) 




BNP 


ISRERR 


ISRDONE 


L 


E5,CCB.DCB(E4) 




LA 


E7,III 




STH 


E7,ISPTAB(E2,E2) 




OC 


E2, DISARM 




LCS 


E6,l 




STH 


E6,DCB.T0UT(E5) 




L 


E7,DCB.LEAF(E5) 




ATL 


E7,SQ 




LPSWR 


EO 


ISRERR 


EQU 


* 




LHI 


E6 / X'8484' 



COMM-MUX command 1 

kill interrupts on COMM-MUX 



come here when buffer done: 
did all of buffer go out? 
if count not positive, error 
set up the CCB for third ISR 

* to be used. 

set command word for buffer 1 
* 

get 1st char from user's buffer 
and send to device 
exit to wait for I/O 

come here when buffer 1 done: 
did all of buffer 1 go out? 
if count not positive, error 
set up CCB to point to last 

* ISR routine to be used 
set up CCB for different 

* buffer pointers 

now get the value for the 

* count field, and then set 

* it up. 

get 1st char from suffix buffer 
and send it to device 
exit to wait for I/O 

come here when all I/O done 

check that all of the last 

transfer completed. 

get address of DCB of device 

clear the interrupt path 

* 

kill device interrupts 
indicate no time-out occurred 
* 

schedule the termination 

* routine for execution 
and exit interrupt service, 
come here if I/O fails 

set a status code for ESR 
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STH E6,CCB.MISC(E4) 
B ISRDONE 
IMPUR 
TERMDRV7 EQU * 



& go exit ISR sequence 

operating system enters here when I/O done 



* The error checking sequence is somewhat arbitrary. Here, a time-out is 

* the most important error; and failure to complete the transfer will be 

* less important. 



get current time-out value 
error exit if timed- out 
get CCB address, 
check error indicator 
if not zero, I/O failed 
otherwise, indicate no error, 
set error status 
indicate no more timing. 



LH 


UO,DCB.TOUT(UD) 


BZ 


TIME0UT7 


LH 


UCDCB.CCB(UD) 


LH 


UO,CCB.MISC(UC) 


BNZ 


I0FAIL7 


LIS 


U1,0 


TERM7B STH 


U1,DCB.STAT(UD) 


BAL 


U8,T0CH0FF 



* By design choice, we will report the length of transfer as only that part 

* of the user's buffer that was actually transferred. We use the count 

* value for buffer 1 for this calculation: 



TIME0UT7 



I0FAIL7 



L 

S 

AH 

ST 

B 

EQU 

LHI 

B 

EQU 

LHI 

B 

ALIGN 



UO,DCB.EADR(UD) 
U0,DCB.SADR(UD) 
U0,CCB.LB1(UC) 
U0,DCB.LLXF(UD) 

IODONE 
* 

U1,X'8282' 
TERM7B 

U1,X'8484' 
TERM7B 

4 



get user's end address 

less user's start address 

plus the residual buffer 1 count 

equals count of bytes moved. 

go to operating system I/O termination 

set time-out status 

* 

set I/O failed status 

* 



* Define 
* 

PREFIX. S 
PREFIX. E 
SUFFIX. S 

SUFFIX. E 



the suffix and prefix output by this driver 



DC 

EQU 

DC 

DB 

EQU 

END 



C'<PREFIX>* 

*-l 

C'<SUFFIX>' 

X * 00 ' , X ' OD ' , X ' 00 ' , X ' OA* , X ' 00 ' , X ' 00 ' 

*-l 
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Step 8: Generating User-Level Task Traps 

In special circumstances, it is desirable to have the device driver add an item to the user's task 
queue, thereby generating a task trap. This feature is most likely to be used in applications that 
require buffer chaining, so that the u-task can be notified each time a data buffer has been processed 
by the driver. 

The following small driver has been written to illustrate the code sequence required to add items to 
the user's task queue, and thus generate user-level task traps. This particular driver causes an item 
to be added to the user's task queue each time an I/O request is made to the driver. Note that this 
sample driver does not interface to a physical device; this is only because a physical device interface 
is not necessary in order to illustrate the add to task queue mechanism. 



INITDRV8 EQU 

L 

LI 

BAL 

* 

B 
TERMDRV8 EQU 



U9,DCB.TCB(UD) 
UA, QUE ITEM 
U8 , TMATQ1 



IODONE 
* 



entry from operating system 

get user ' s TCB address 

get value to put on task queue 

branch to operating system 

routine to add item to 

the task queue . 

exit from driver. 

not executed: used to 

satisfy reference from 

DCB.TERM entry in DCB. 



QUE ITEM EQU 
END 



(item definition is arbitrary) 



It should be noted that the routine "TMATQ1" is subject to being renamed in future revisions of the 
operating system. In revision 6.2 and lower, the label was "SV9.ATQ1". For this reason, the writer 
of a driver may want to replace the statement: 

BAL U8 , TMATQ1 
with the macro call: 

ADDTTSKQ REASON= (UA) , TASKSW=NO 
This coding practice assures compatability with future releases of the operating system. 

Step 9: Making Changes for IOP Execution 

The following two drivers operate identically. However, the first driver does not execute correctly 
on an IOP. The second driver contains calls to the new macros needed to generate code that operate 
correctly under an IOP. 
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INITDUMB PROG DUMMY DRIVER FOR OS/32 REVISION 7. 

* 

* THIS DRIVER WILL NOT OPERATE CORRECTLY ON AN IOP 



MLIBS 8,9,10 

ENTRY INITDUMB DRIVER INITIALIZATION 

ENTRY TERMDUMB DRIVER TERMINATION 

EXTRN DIRDONE, IODONE, SQ, III, I SPTAB 
INITDUMB EQU * 



LH U2,DCB.DN(UD) 

LA UF,III 

STH UE,ISPTAB(U2,U2) 

L UF , DCB . LEAF (UD) 

ATL UF , SQ 

B DIRDONE 



GET THE DEVICE ADDRESS. 

SET NULL INTERRUPT VECTOR 

FOR THE DEVICE. 

GET LEAF TO SCHEDULE TERMINATION 

BY PUTTING IT ON SYSTEM QUEUE. 

EXIT TO OS ROUTINE. 



TERMDUMB EQU 
B 



IODONE 



DRIVER IS DONE - QUIT NOW. 



INITDUMB PROG DUMMY DRIVER FOR OS/32 REVISION 8. 

* THIS CODE WILL EXECUTE CORRECTLY ON AN IOP 
* 

MLIBS 8,9,10 

ENTRY INITDUMB DRIVER INITIALIZATION 

ENTRY TERMDUMB DRIVER TERMINATION 

EXTRN DIRDONE , I ODONE , SQ , I I I , I SPTAB 
INITDUMB EQU * 

LH U2,DCB.DN(UD) GET THE DEVICE ADDRESS. 

LA U6,III GET THE NULL INTERRUPT VECTOR. 

ISPMOD ITEM= (U6) , DCB= (UD) ,DN=(U2) ,WORK=(UF) 

L UF, DCB. LEAF (UD) GET LEAF TO SCHEDULE TERMINATION 

ADDSQ ITEM= (UF) , DCB= (UD) , WORK= (UE) 

B DIRDONE EXIT TO OS ROUTINE. 

* 



TERMDUMB EQU 
B 



IODONE 



DRIVER IS DONE - QUIT NOW. 
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2.3 WRITING DEVICE CONTROL BLOCK/CHANNEL CONTROL BLOCK (DCB/CCB) 
SPECIFICATIONS 

Every device driver operates primarily on two associated data structures, the DCB and the CCB. It 
is the responsibility of the writer of the I/O driver to provide definitions of these two data 
structures, along with the actual I/O driver. The remainder of this chapter provides some procedures 
for specifying the DCB and CCB structures. 

It is very important that the DCB and CCB specification be done exactly right the first time! An 
error in the DCB or CCB specification can result in any of the following symptoms: 

1. Errors in the Sysgen32 phase of the sysgen procedure. 

2. Errors in the macro expansion phase of the sysgen procedure. 

3. Errors in the CAL assembly phase of the sysgen procedure. 

4. Errors in the link phase of the sysgen procedure. 

5. System crashes of all kinds when attempting to use the driver. 

6. Other malfunctions of the driver. 

The DCB definition contains all of the keyword definitions which can be used in the sysgen 
statement, such as the device name, device address, device code, controller address, SELCH 
address, and extended device codes. The DCB definition also provides a definition of all of the 
device-dependent data items that can be referenced by the driver, such as (for disks) the number of 
sectors per track, tracks per cylinder and cylinders per disk. Other device-dependent data can 
include special command tables for setting baud rates on asynchronous lines, and tables of tape 
motion speeds for magnetic tape drives. For some devices, data buffers or scratchpads can be 
included in the DCB definition. 

Fortunately, most custom devices can utilize a DCB definition that is very nearly the same as a 
DCB definition already provided for a standard Perkin-Elmer device. Due to the large amount of 
detail that must be provided in the DCB definition, the best way to build a new DCB definition is to 
start with an existing DCB definition. The following steps provide a guide for building a new DCB 
definition: 

1. Copy a DCB specification of a similar type of device from SYSGEN32.MLB into a new file, 
DCBxxx.MAC (xxx is the new device code, which must be in the range of 240 to 255). This 
can be done using MLU32, and listing the appropriate macro definition directly to 
DCBxxx.MAC. For example, a device that operates under a SELCH and supports both read 
and write, but does not support random access, is similar to a magnetic tape drive, so the 
macro definition DCB65 would probably be a good starting point. For example, the following 
session copies the definition of a magnetic tape driver into a file named DCB248.MAC: 
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*lo mlu32;st 

PERKIN-ELMER OS/32 MACRO LIBRARY UTILITY 03-340 ROO-01 

MLU>get sysgen32 .mlb/s 

MLU>list deb 2 48. mac ,00864 

1 MACRO LISTED TO NEW FILE SYS :DCB248 .MAC 

MLU>end 

RW -END OF TASK CODE= PROCESSORS. 907 TSK-ELAPSED=38 

2. In DCBxxx.MAC, change the DCB number (e.g., 65), to the new device code (e.g., 240) 
everywhere that it appears. Be careful not to miss any appearances of the old DCB number, 
but also be careful (if you are using EDIT32) not to modify any other character strings that 
just happen to match the new DCB number (e.g., 240). 

3. After the line: 

C0NVNUM 
Add the statement: 

USERINIT 

4. Modify the parameters for the DCBI macro statement. This includes at least the INIT= and 
TERM= parameters, and probably the ATRB= parameter. This macro call specifies the values 
assumed by various data items within the DCB. Look over the DCBI macro statement 
carefully to be sure that you have adjusted all the terms that apply to your specific custom 
device. The device-dependent part of the DCB is specified in the DCBI macro statement with 
a COPY= parameter. 

5. It is very unlikely that you will need to modify the CCBI macro statement, other than what 
was done in Step 2 above. The CCB is usually set up at run time by the driver. The possible 
exception would be a translation table name. 

6. Add the statement 

DCB%DCOD%IDVAL PROG USER DCB 

after the CCBI macro statement, as shown in the example below. This provides a label that 
prints when the macro is assembled at sysgen time. This is a handy way to know if your DCB 
definition successfully passed that particular stage of the sysgen procedure. 
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7. Add the definition of any specific values in the device-dependent portion of the driver. This is 
done by the following constructs, which should be placed immediately preceding the 
$ST%OFFS statement near the end of the DCBxxx.MAC file: 

ORG DCB%OFFS+DCB.yyyy 
DC 

The label DCB.yyyy is a label defined in the device-dependent part of the DCB. The existence 
i of the label, and its assigned value, are determined strictly by the requirements of your 

specific custom device. 

8. After the statement 

ORG $ST%OFFS 

Add the statements: 

ASIS 
END 

If these eight steps are carefully done, the DCB definition will be complete. 

To use the new DCB definition, which has been created in the file DCBxxx.MAC, it must be put 
into a macro library known as USERDLIB.MLB. This is done by using the MLU32 utility program. 

Note that the device-dependent part of the DCB is determined by the specific requirements of 
your driver. In general, write your driver code first to determine what, if any, specific device- 
dependent fields you need, then include them in your DCB definition. 

For programmers who are familiar with the now unsupported Configuration Utility Program 
(CUP), it is important to know that the use of Sysgen/32 requires that the DCB and the actual 
driver code be constructed in separate files, and placed in separate libraries. This is considerably 
different from the procedures used with CUP. The Sysgen/32 procedures require that the DCBxxx 
macro definition be placed in a macro library, USERDLIB.MLB; the driver code is expanded, 
assembled, and included in object format in an object library, USERDLIB.LIB. After this is done, 
the supplied SYSGEN.CSS can be used to perform the sysgen. 

The major item of concern in writing the DCBXXX macro is the specification of the DCB 
macro. This macro defines the initialization, termination, function, and IOH routines used by 
the driver. Also specified here is the device code, attributes, and size of the DCB. 
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The DCB specification macro: 

DCB DCOD = ,INIT = , TERM =, ATRB = ,RECL = ,SIZE = , IOH = 

DCOD - DCB number (gives each device type a unique code) 

INIT - entry point to driver initialization routine. 

TERM - name of first ESR to execute. 

ATRB - attributes of the device 



RECL - record length supported by the device 

SIZE - size of the driver + dependent structures 

IOH - name of I/O handler for this device. 
A sample DCBXXX macro to be included in USERDLIB.MLB: 

MACRO 

DCB243 %DCOD=, %DN=, %CLAS=, %ILVL=, %NAME=, %SHCCB= / 
%SIZE=, %RECLN=, %XDCD=, %IOP=0 

GBLC %IDVAL 

BGBLA %ID243 

LCLA %CCBFL 

LCLA %CLASN 

LCLC %RXLT,%RQU 

LCLC %CORDNM,%PTRPAS 

LCLC %OFFS 

LCLA %RDN 

LCLC %MDN , %MCNT , %MSLCH 

LCLA %TRCNT,%UPTR 

LCLB %FOUND / %DA 

BGBLA %FIRST 
%RQU SETC * COMQ ' 
%MDN SETC '%DN' 
%CCBFL SETA 

AIF (T'%CLAS EQ 'U')&CLSNTD 
%CLASN SETA %CLAS*12 I0CLASS*12 



DEFAULT DEVICE QHANDLER 
DEVICE ADDRESS 
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CONVERT CURRENT ID TO HEX. 



&CLSNTD ANOP 

CONVNUM VAL=%ID243 

USERINIT 

$DCB$ 

DCBI DCOD=243, SIZE=DCB.DVDP, INIT=INITCORD, IOC=2, 

TERM=TERMCORD, FLGS=DFLG. LNM, RECL=132 , ID=%IDVAL / 
ATRB=2B80, IOP=%IOP 



x 
x 



CCBI 
CCB%NAME EQU 
%ID243 SETA 
&DCBOPT ANOP 
DCB%DCOD%IDVAL 
%OFFS SETC 
DCB_%NAME EQU 



DCOD=243, ID=%IDVAL 

CCB%DCOD%IDVAL 

%ID243+1 



PROG USER DCB 
•%DCOD' : *%IDVAL' 
DCB%OFFS 
ENTRY DCB_%NAME 
ORG DCB%OFFS+DCB.DN 
H'%DN' 
DCB%OFFS+DCB.LEAF 



ESTABLISH PROPER OFFSET 



DEVICE ADDRESS 



DC 
ORG 
AIF 
DAC 



LEAF POINTER 



&NSLEAF 



&NRMLFX 
&NOLEAF 



&NOCLAS 



&NOILVL 
AIF 
ORG 
DC 



(T'%SHCCB' EQ 'U')&NSLEAF B IF NOT SHARED 
LF%SHCCB USE SHARED DEVICE LEAF 

EXTRN LF%SHCCB 
AGO &NRMLFX 
ANOP 

DAC LF%OFFS GENERATE STANDARD LEAF NAME 

EXTRN LF%OFFS 
ANOP 
ANOP 
AIF 
ORG 
DC 
ANOP 
AIF 
ORG 
DC 
ANOP 

(T'%XDCD EQ 'U')&NOXDCD 



(T'%CLAS EQ 'U')&NOCLAS 
DCB%OFFS+DCB.CLAS 10 CLASS 
H*%CLASN' I0CLASS*12 



(T'%ILVL EQ 'U')&NOILVL 
DCB%OFFS+DCB. ILVL 
H'%ILVL' 



ILEVEL 



DCB%OFFS+DCB.XOPT 
%XDCD 



IF NOT ENTERED 

ELSE MOVE XDCD 
EXTENDED DCOD 
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&NOXDCD ANOP 

ORG DCB%OFFS+DCB.DMT 

DC DMT_%NAME A (DMT ENTRY) 

EXTRN DMT_%NAME 

AIF ('%ROU' EQ ")&NOQU 

ORG DCB%OFFS+DCB.Q 

DAC %RQU 

EXTRN %RQU 
&NOQU ANOP 

AIF (T'%RECLN EQ 'U')&NORECLN 

ORG DCB%OFFS+DCB.RECL RECORD SIZE 

DC H'%RECLN' 
&NORECLN ANOP 

ORG $ST%OFFS ORG TO END OF DCB 

ASIS 

END 
%RDN SETA %DN+1 

MEND 
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CHAPTER 3 
INCLUDING THE DRIVER IN YOUR OPERATING SYSTEM 



3.1 INTRODUCTION 

Special procedures are necessary at system generation (sysgen) time to include the driver into your 
operating system. These include expanding and assembling the driver before incorporating the 
driver into the sysgen configuration. Please note that although the Configuration Utility Program 
(CUP) is no longer supported, instructions for sysgening with CUPMT have been included for those 
users who work with older versions of OS/32. 

3.2 EXPANDING AND ASSEMBLING DRIVERS 

The conventional name for operating system and driver source modules is XXXX.MAC 
(where XXXX is a symbolic name for the device which the driver controls). The command 
substitution system (CSS) procedures which follow are typical procedures which can be used; 
however, these can be modified for individual installations. 

*EXPAND.CSS <name of module - (XXXX) > 

XAL @l.CAL,IN,80/8 

L .BG,MACR032,50 

T .BG 

AS 1,@1.MAC,SR0 

AS 2,@1.CAL 

AS 3, NULL: (this is the list file) 

AS 7, SYSGEN. MAC/S,SRO 

AS 8 , SYSSTRUC . MLB/S , SRO 

AS 9,SYSMACR0.MLB/S,SR0 

AS 10, DVRM. MLB/S, SRO 

AS 11, ITMS. MLB/S, SRO 

AS 1 2 , S YSMAC3 2 . MLB/S , SRO 

ST,MLIBS= (8, 9, 10, 11, 12) 

SEXIT 
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*ASSEMBLE.CSS <name of module - (XXXX) > 

XAL @1. OBJ, IN, 126 

XAL @1.LST, IN, 132/10 

L .BG,CAL32,80 

T .BG 

AS 1,@1.CAL,SR0 

AS 2,@1.0BJ 

AS 3,@1.LST 

ST, CROSS, SQUEZ, NLSTM, NUREX, NLSTU 

$EXIT 

The above code expands and assembles both CUP- and Sysgen/32-generated drivers. However, if it 
is Sysgen/32, the device control block (DCB) requires special code which is explained below. 

After the macro definition for the device is prepared, it must be included in the user's macro 
library. If this library, USERDLIB.MLB, does not currently exist, it must be created by the macro 
library utility. 

r 

L MLU32 
ST 

> ESTABLISH USERDLIB.MLB 

> INCLUDE DCB240.MAC (Include user DCB/CCB definition) 

> S* 

> END 

If the macro library already exists, use the GET command rather than the ESTABLISH command. 
If you are replacing DCB240 with a newer version, use the DELETE command before you do the 
include. 

L MLU32 
ST 

> GET USERDLIB.MLB 

> DIR (this lists all macros in the library 
DCB240 

> DELETE DCB240 

> INCLUDE DCB240.MAC (include the new DCB/CCB definition) 

> S* 

> END 

For CUPMT-generated systems, it is a requirement that the NUREX option to Common Assembly 
Language/32 (CAL/32) be used. If this option is not used, FRMT errors from CUPMT may be 
generated. 
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3.3 SYSTEM GENERATION (SYSGEN) WITH CUPMT 

For those users who have software release R06 or lower, this section is necessary. If you have 
software release R07 or higher, you may continue on to Section 3.4. 

The following is a discussion of the relationship of the statements in the CUP file to elements in the 
DCB. 

♦Sample device configuration statement in CUP file. 

1 DEV:64,247 

where: 

1 is a control number for CUP 

DEV is the device mnemonic name by which the user references the device 

through the "assign" function. This does NOT appear in the DCB. However, 
the address where this name can be found appears at DCB.DMT. 

64 is the physical device address is determined by the hardware configuration. 

This entry in the configuration statement must agree with hardware address 
settings. This value appears in the DCB as the 16-bit (halfword) value 
DCB.DN. 

247 is the device type code that is defined in the DCB.DCOD field. This is the 

code used by CUP to select a particular device driver. The DCB definition 
statement DCB DCOD=247 corresponds to this value. 

To build a new version of OS/32 incorporating a custom device interface, the following files are 
required. AH of these files, with the exception of USERDLIB.LIB (the file you will build to 
contain your driver) are supplied by Perkin-Elmer with OS/32: 



SYSGEN1.CSS SYS. LIB CUPMT. TSK 

SYSGEN2.CSS ITBSYS.LIB LIBLDR.TSK 

SYSGEN3.CSS DRIVER. LIB LINK. TSK 

ITBDLIB.LIB 

UBOT . OBJ 

USERDLIB.LIB 

configuration file 

The "SYSGEN1" procedure provided with OS/32 software packages assumes that all customer- 
provided drivers are contained in a file named USERDLIB.LIB, in whatever account is used for 
doing the sysgen procedure. Therefore, the incorporation of customer drivers requires only that 
the customer driver source file be macro-expanded, assembled and the resultant object file be 
placed in a file known as USERDLIB.LIB. These procedures can be customized to your 
installation (i.e. list files can be assigned instead of the printers, etc.) The following procedure 
can be used to build USERDLIB.LIB. 
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SBUILD USERDLIB.CMD 

FI 2 DCBXXX 

CO 2,1 

RW 2 

CO 2,1 

END 

$ENDB 

L .BG,LIBDLR 

T .BG 

AS 1,USERDLIB.LIB 

AS 2,DRVR.OBJ,SRO 

AS 5, USERDLIB.CMD 

ST 

The following is a sample of a configuration file: 



ACCOUNTING 4 

VERSION 11-18-83 

CPU 3210 

MEMORY 4096 

CLOCK 60,6C,6D 

BACKGROUND 128,50 

CMDLEN 80 

CSS 8 

DATE MMDDYY 

DEVADS 

DIRECTORY 

DISCBLOCK 255 

DSYS 200 

ERRORREC SYS rERR0R.LOG, 200, 5 

FLOAT H,H 

ITAM 

JOURNAL O 

LOGLEN 80 

MAXTASK 40 

MODULE 

INTC.F02 

ENDM 

ROLL SYS 

SPOOL SYS 

TEMP SYS 

VOLUME SYS 

DEVICES 



* 3210 

* 3210 WITH 8 REGISTER SETS 

* 4 MEGABYTES OF MEMORY 

* STANDARD CLOCK ADDRESSES 

* .BG MAXPRI=128,MAXSYS1-50KB 

* COMMAND LENGTH = 80 BYTES 

* CSS NESTING LEVEL = 8 

* U.S. DATE FORMAT 

* MAX DEVICE ADDR = X'FF' 

* CORE DIRECTORY SUPPORT 

* MAX BLOCK SIZE = 255 SECTORS 

* SYS SPACE ALLOCATION 

* SUPPORT MEMORY ERROR LOGGING 

* SOFTWARE FLOATING POINT 

* NO JOURNAL SUPPORT 

* LOG MESSAGE BUFFER LENGTH 

* 40 CONCURRENT TASKS 



* ROLL VOLUME = SYS 

* SPOOL VOLUME = SYS 

* TEMP VOLUME = SYS 

* SYSTEM VOLUME = SYS 

* BEGIN DEVICE STATEMENTS 
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1 C0N:10,39,C,XD 
1 CRT1 112,39, ,XD 
1 CRT2:20,39, , XD 
1 CRT3:22,39, , XD 
1 CRT4:24,39, , XD 

i crts:26,39, ,XD 
i crt6:28,39, ,xd 

1 CRT7:2A,39, ,XD 

1 CRT8: 20,39, , XD 

1 CRT9:2E,39, , XD 

1 LP:62,113 

1 PR:0,0,S 

1:F1,0 

2:0,0 

3 MAG1:C5,70 

2:EB,0 

3 D80:EC,53,D 

3 D300:ED,54,D 

1 XXXX:64,247 

ENDD 

ENDC 

First Step of Sysgcn Procedure: 



* CONSOLE -550 ON COM-MUX 

* CRT AT ADDRESS X'12' 

* CRT AT ADDRESS X'20' 



* LINE PRINTER 

* SPOOL DEVICE 

* SELCH El- -FOR DISK DEVICES 

* MAG TAPE CONTROLLER 

* 6250 BPI TELEX TAPE AT X*c5' 



* user developed device 



**SYSGEN1.CSS 



[CUP ED] , [SEGSIZE] 



$IFNULL @1 

$WR ***@0: CONFIGURATION STATEMENT FD OMITTED 

$CLEAR 
$ENDC 
EXIST @1 

EXIST DRIVER. LIB/S • 
EXIST ITBDLIB. LIB/S 
XDE CUPOUT.OBJ 
AL CUPOUT.OBJ, IN, 12 6/2 
$IFNULL @2 

LO .BG,CUPMT 
$ELSE 

LO .BG,CUPMT,@2 
$ENDC 
TA .BG 
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AS 1,@1,SR0 

AS 2,CUP0UT.0BJ 

AS 3, PR: 

$IFX USERDLIB.LIB 

AS 4, USERDLIB.LIB, SRO 
$ELSE 

AS 4, NULL: 
$ENDC 

AS 5, DRIVER. LIB/S, SRO 
$IEX ITED2780.LIB/S 

AS 6 / ITED278O.LIB/S / SR0 
$ELSE 

AS 6, NULL: 
$ENDC 
$IFX ITEDZDLC.LIB/S 

AS 7, ITEDZDLC.LIB/S, SRO 
$ELSE 

AS 7, NULL: 
$ENDC 
$IFX ITED327S.LIB/S 

AS 8,ITED327S.LIB/S,SRO 
$ELSE 

AS 8, NULL: 
$ENDC 
$IFX ITED327E.LIB/S 

AS 9,ITED327E.LIB/S,SR0 
$ELSE 

AS 9, NULL: 
$ENDC 
$IFX ITBDLIB.LIB/S 

AS 10, ITBDLIB.LIB/S, SRO 
$ELSE 

AS 10, NULL: 
$ENDC 
$IFX DRIVER. LIB/S 

AS 11, DRIVER. LIB/S, SRO 
$ELSE 

AS 11, NULL: 
$ENDC 
START 
$IFNE 

$WR ***@0: ERRORS DETECTED BY CUP 
DEL CUPOUT.OBJ 



3-6 48-190 FOO ROO 



$ CLEAR 
$ENDC 

$WR *** ENTER SYSGEN2 IMPURE, PURE [,SEGSIZE] 
$EXIT 

Second Step of Sysgen Procedure: 

**SYSGEN2.CSS [IMPURE] , [PURE] , [SEGSIZE] 

$IFNULL @1 

$WR ***@0: MISSING PARAMETER (IMPURE BIAS) 

$CLEAR 
$ENDC 
$IFNULL @2 

$WR ***@0: MISSING PARAMETER (PURE BIAS) 

$ CLEAR 
$ENDC 

EXIST SYS.LIB/S 
EXIST ITBSYS.LIB/S 
EXIST UBOT.OBJ/S 
EXIST CUPOUT.OBJ 
XAL LIBLD0UT.0BJ,IN,126 
XDEL LIBLDR.CMD 
$BUILD LIBLDR.CMD 
TO FFFFF 
OU 2 
BI @1 
PB @2 
LO 1 
ED 1 
ED 4 
ED 6 
ED 7 
ED 8 
ED 9 
ED 10 
ED 11 
ED 12 
ED 13 
XO 

MA 3 
AM 3 
EN 
$ENDB 
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SIFNULL @3 

LO .BCLIBLDR 
$ELSE 

LO .BG,LIBLDR,@3 
$ENDC 
TA .BG 

AS l,CUPOUT.OBJ 
AS 2,LIBLDOUT.OBJ 
AS 3, PR: 

AS 5,LIBLDR.CMD,SR0 
AS 4,SYS.LIB/S,SR0 
$IFX USERSYS.LIB 

AS 6, USERSYS.LIB, SRO 
$ELSE 

AS 6, NULL: 
$ENDC 
$IFX ITES2780.LIB/S 

AS 7,ITES2780.LIB/S,SRO 
$ELSE 

AS 7, NULL: 
$ENDC 
$IFX ITESZDLC.LIB/S 

AS 8, ITESZDLC.LIB/S, SRO 
$ELSE 

AS 8, NULL: 
$ENDC 
$IFX ITES327S.LIB/S 

AS 9,ITES327S.LIB/S,SRO 
$ELSE 

AS 9, NULL: 
$ENDC 

$IFX ITES327E.LIB/S 
$ELSE 

AS 10, NULL: 
$ENDC 
$IFX MCONFIG.OBJ 

AS 11, MCONFIG.OBJ 
$ELSE 

AS 11, NULL: 
$ENDC 

AS 12,ITBSYS.LIB/S,SR0 
AS 13,UB0T.0BJ/S,SR0 
START 
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$IFNE 

$WR ***@0: ERRORS DETECTED BY LIBLDR 

XDEL LI BLDOUT. OBJ, LIBLDR.CMD 
$ CLEAR 
$ENDC 

XDEL CUPOUT . OBJ , LI BLDR . CMD 
$WR *** ENTER SYSGEN3 , OSFD [,SEGSIZE] 
$EXIT 

Third Step of Sysgen Procedure. 

**SYSGEN3.CSS [] , [OS FD] , [SEGSIZE] 

** 

$IFNULL @2 

$WR ***@0: MISSING PARAMETER (OUTPUT FD) 

$CLEAR 
$ENDC 

EXIST LI BLDOUT. OBJ 
XDEL @2 

$BUILD LINKOS.LNK 
ESTAB OS 
MAP PR: 

INCL LI BLDOUT. OBJ 
BUILD @2 
END 
$ENDB 

$IFNULL @3 
LO .BG^INK 
. $ELSE 
LO .BG^INK^a 
$ENDC 
TA .BG 

ST / C=LINKOS.LNK,L=PR: 
$IFNE 

$WR ***@0: ERRORS DETECTED BY LINK 

XDE LINKOS.LNK ,@2 

$CLEAR 
$ENDC 

XDE LINKOS . LNK , LI BLDOUT . OBJ 
$WR *** OS @2 LINKED *** 
$EXIT 
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3.4 SYSTEM GENERATION (SYSGEN) WITH SYSGEN/32 

The following is a discussion of Sysgen/32 device specification statements. 

The device has the following characteristics: 

Device Name = NEWD 
Address = X'64' 
Device Code = 247 

This device operates on the multiplexor (MUX) bus: 

DEVICES 
NEWD: ,64,247 

ENDD 

DEVICES 

NEWD: , 64, 247, SELCH=FO, CONTR=0 

ENDD 



COPY 

MCALL DCBI , CCBI , CONVNUM 
ENDCOPY 

ACCOUNTING = 4, NOF I LE ACCOUNTING 
BACKGROUND = 128,50 
CLOCK = 60,6C,6D 
CMDLEN = 80 
CPU = 3210 
CSS = 8 
DATE = MMDDYY 
DEVADS = 
DIRECTORY 
DISCBLOCK = 255 
DSYS =1024 

ERRORREC = SYStERR0R.LOG, 1024, 2 
FLOAT = H,H 
I LEVEL = O 
INTERCEPT 
IREADER 
IT AM 

JOURNAL = 
LOGLEN = 80 
MAXTASK = 32 

MCONF I G BLOCK=0 , START=0 , RANGE= 
MEMCHECK 
MEMORY = 4096 



,EVNGEN,MMDGEN 

*4 accounting classes 
* .bg maxpri=128, sys=50KB 
♦standard clock addresses 
*80 byte command buffer 
♦processor model 3210 
*8 levels of CSS nesting 
*U.S.A. date format 
♦less than 256 devices 
♦secondary directory support 
♦permit max blocking 
♦1 MB of system space 
♦error log readout . . 2 min. 
♦hardware floating point 
♦all interrupts on level 
♦permit SVC interception 
♦permits use of SVC 2,14 

♦don't waste time on journal 
♦message buffer size 
♦default for max# of tasks 
4,INTERL=0 ♦mem config for err log 
♦verify mem exists at IPL 
♦4 MB system 
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SPL32 * spool 3 2 support 

SSTABLE = 32 *shared segment tbl entries 

TEMP = SYS *temp volume = 'SYS* 

VERSION = OS321212 *6.2 os build on Dec 12. 

VOLUME = SYS *system volume = *SYS' 

DEVICES * BEGIN DEVICE STATEMENTS 

* System console. 

CON:, 10, 39, CONSOLE, CLOCK=XD *system console-fast clock 

* Crt type devices . 

* a. Non-bioc CRT driver is selected by USER= (CRT=1) . 

* b. Fast clock is selected by XD. 
NEC : , 12 , 40 , REC=132 , SIZ=66 , XD=X6966 
IPC : , 12 , 39 , REC=132 , CL0CK=XB 

CRT2 : , 20, 156 , XDC=X0030, RECL=132 , PAD=3 

WP02 : , 20, 39, CL0CK=XD 

CRT3 : , 22 , 156 , XDC=X0030 , RECL=132 , PAD=3 

WP03 : , 22 , 39 , CL0CK=XD 

CRT4 : , 24, 156 , XDC=X0030, RECL=132 , PAD=3 

WP04 : , 24 , 39 , CL0CK=XD 

CRT5: , 26,156,XDC=X0030,RECL=132,PAD=3 

WP05 : , 26 , 39 , CL0CK=XD 

CRT6 : , 28 , 156 , XDC=X0030 , RECL=132 , PAD=3 

WP06 : , 28 , 39 , CL0CK=XD 

CRT7: , 2A, 156, XDC=X0030,RECL=132,PAD=3 

WP07 : , 2A, 39, CL0CK=XD 

*CRT8 : , 2C, 156, XDC=X0030, RECL=132 , PAD=3 

MODA: , 2C,156,XD=X0810,RECL=132 

WP08 : , 2C, 39, CL0CK=XD 

CRT9: , 2E, 156,XDC=X0030,RECL=132,PAD=3 

WP09 : , 2E , 39 , CL0CK=XD 

♦printers 

LP: ,62,113 

D80A: ,EC,53,SELCH=F1,C0NTR=EB 

D300: ,ED,54,SELCH=F1,C0NTR=EB 

MAGI : , C5 , 68 , SELCH=F1 , C0NTR=0 

XXXX:,64,247 *user developed device 

ENDD 

ENDC 

Once the specifications have been placed in the configuration file (named xxxxxxxx.sys), sysgen is 
performed by typing SYSGEN xxxxxxxxx, from account 0. The procedures can be modified to look 
for the macro libraries and other files required on any account which you choose. The following 
procedures are used with Sysgen/32 for the sysgen procedure: 
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@1 = CONFIGURATION STATEMENT INPUT FILE 

@2 = CORE INCREMENT FOR SYSGEN32 TASK 

@3 = VOLUME FOR LIBRARIES (.MLB & .LIB) 

@4 = MACRO AND CAL LISTING FLAG. @1.PRT FILENAME 

USED DEFAULT IS ERROR MESSAGES TO @1.PRT ONLY. 
@5 = FILE SAVE FLAG. CSS WILL SAVE ALL INTERMEDIATE 

FILES CREATED IN THE SYSGEN PROCESS. DEFAULT IS 

TO DELETE ALL INTERMEDIATE FILES. 
@6 = MACRO & CAL LIST FILE- DEFAULT IS @1.PRT 

SYSGEN. CSS 

STATEMENT FORMAT: SYSGEN CS, CI , V,LF, SF,MCL 
* 

* 

* 
* 

* 
* 
* 

* 



CS = CONFIGURATION STATEMENT INPUT FILE 
CI = CORE INCREMENT FOR SYSGEN32 TASK 
V = VOLUME FOR LIBRARIES (.MLB & .LIB) 
LF = MACRO AND CAL LISTING FLAG. 

DEFAULT IS ONLY ERROR MESSAGES TO @1.PRT. 
SF = FILE SAVE FLAG. CSS WILL SAVE ALL 

FILES CREATED IN THE SYSGEN PROCESS. 

DEFAULT IS TO DELETE ALL INTERMEDIATE FILES. 
MCL= MACRO & CAL LIST FILE- DEFAULT IS 'CS'.PRT 



EXAMPLE: 



SYSGEN OS32SYS,30,M300: / , ,CON; 



(REQUIRED) 
(OPTIONAL) 
(OPTIONAL) 
(OPTIONAL) 

(OPTIONAL) 



(OPTIONAL) 



** SYSGEN. CSS 

* * 

** THIS CSS IS THE FIRST ONE USED TO RUN THE SYSGEN32 PROCEDURE 

* * 

* * 

* * 

* * 

* * 

* * 

* * 

* * 

* * 

* * 

$WR * 

$WR * 

$WR * 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 

$WR 



(REQUIRED) 
(OPTIONAL) 
(OPTIONAL) 
(OPTIONAL) 

(OPTIONAL) 



(OPTIONAL) 



$CL;$ENDC 



SYSGEN32 @1,@2 



**SYSGEN32.CSS 
** 

** THIS CSS IS USED TO RUN THE FIRST PART OF SYSGEN32 PROCEDURE 
* * 



** @1 = CONFIGURATION STATEMENT INPUT FILE 
** @2 = SIZE INCREMENT FOR TASK 



(REQUIRED) 
(OPTIONAL) 



$IFNULL @1; $WR *** INPUT FILENAME MISSING ***; $CLEAR; $ENDC 

$IFNX @1.SYS 

$WR *** INPUT FILE @1.SYS DOES NOT EXIT, SYSGEN32 ABORTED ***; $CL 
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$ENDC 

XDE @1.MAC 

XAL @1.LST, IN, 132/5 

$IFNULL @2 

LO •BG / SYSGEN32; TA .BG 

$ELSE 

LO .BG,SYSGEN32,@2; TA .BG 

$ENDC 

ST , I N=@l . SYS , OUT=@l . MAC , LI ST=@1 . LST 

$IFNE 0; $WR *** SYSGEN32 ERROR ***; $CLEAR; $ENDC 

$EXIT 

SYSMACRO @1,@3,@4,@5,@6 

SYSLINK @1,@3,@5 

$EXIT 

** SYSMACRO. CSS 

* * 

** THIS CSS IS THE SECOND ONE USED IN THE SYSGEN32 PROCEDURE 

** IT WILL EXPAND AND ASSEMBLE THE MACROS GENERATED BY SYSGEN32 

* * 

** @1 = CONFIGURATION INPUT FILE NAME (REQUIRED) 

** @2 = VOLUME WITH MACRO LIBRARIES (OPTIONAL) 

** @3 = LISTING PROVIDED IF NOT NULL (OPTIONAL) 

** @4 = DO NOT DELETE FILES (OPTIONAL) 

** @5 = LIST FILE- DEFAULT IS @1.PRT (OPTIONAL) 

* * 

$IFNULL @1; $WR *** INPUT FILENAME MISSING ***; $CLEAR; $ENDC 

$IFNX @1.MAC 

$WR *** MACRO FILE @1.MAC DOES NOT EXIST, SYSGEN ABORTED ***; $CL 

$ENDC 

XAL @1.CAL, IN, 80/20 

LO .BG,MACR032/S,50; TA . BG 

AS 1,@1.MAC,SR0 

AS 2,@1.CAL,EW0 

SIFNULL @5 

XAL @1.PRT,IN,132 

AS 3,@1.PRT,SW0 

$ELSE 

AS 3,@5,SW0;$ENDC 

MLBCK @2SYSGEN32,8 

MLBCK @2DVRM,9 

MLBCK @2ITMS,10 

MLBCK @2SYSSTRUC,11 

MLBCK @2 SYSMACRO, 12 



48-190 FOO ROO 3-13 



*MLBCK @2ITED327S,13 

*MLBCK @2ITED327E,14 

$IFX USERDLIB.MLB 

AS 7,USERDLIB.MLB,SRQ 

$IFNULL @3 

ST ,MLIB=(7,8,9,10,11,12) , BATCH, MLIST= (ND,NG) 

* ST ,MLIB=(7,8,9,10,11,12,13,14) , BATCH, MLIST= (ND,NG) 
$ELSE 

ST ,MLIB=(7,8,9,10,11,12) , BATCH 

* ST ,MLIB=(7,8,9,10,11,12,13,14) , BATCH 
$ENDC 

$ELSE 

$IFNULL @3 

ST ,MLIB=(8,9,10,11,12) , BATCH, MLIST= (ND,NG) 

* ST ,MLIB=(8,9,10,11,12,13,14),BATCH,MLIST=(ND,NG) 
$ELSE 

ST ,MLIB=(8,9,10,11,12) , BATCH 

* ST ,MLIB=(8,9,10,11,12,13,14) , BATCH 
$ENDC 

$ENDC 

$IFNE 

$WR *** ERRORS IN MACRO EXPANSION, SYSGEN ABORTED ***; $CL 

$ENDC 
*** 

*** ASSEMBLE THE EXPANDED MACRO CODE **** 
** * 

$IFNULL @4; XDE @1.MAC; $ENDC 

XAL @1.0BJ, IN, 126/5 

LO .BG,CAL32/S,50; TA .BG 

AS l,@l.CAL,SRO 

AS 2,@1.0BJ,EWO 

$IFNULL @5 

AS 3,@l.PRT,SWO 

$ELSE 

AS 3,@5,SWO;$ENDC 

TE 5, IN, 256/5/10 

$IFNULL @3; ST , BATCH, NOSQZ, NLIST 

$ELSE; ST , BATCH, NOSQZ, NLSTU, NFREZ; $ENDC 

$IFNE 

$WR *** ERRORS IN ASSEMBLY, SYSGEN ABORTED ***: $CL 

$ENDC 

$IFNULL @4; XDE @1.CAL; XDE @1.PRT; $ENDC 

$EXIT 
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**SYSLINK.CSS 
* * 



** THIS CSS IS THE LAST USED IN THE SYSGEN PROCEDURE 

** IT WILL LINK THE OBJECT CREATED BY CAL WITH THE APPROPRIATE 

** LIBRARIES TO PRODUCE THE OS. THE MAP FOR THE OS WILL BE 

** APPENDED TO THE LIST FILE. 



** @1 = CONFIGURATION INPUT FILE NAME (REQUIRED) 

** @2 = VOLUME WHERE SYSTEM AND DRIVER LIBRARIES RESIDE (OPTIONAL) 

** @3 = SAVE LINK CMD FILE - DEFAULT IS DELETE (OPTIONAL) 

** 

$IFNULL @1 

$WR *** INPUT FILENAME MISSING *** 

$CLEAR 

$ENDC 

$IFNX @1.0BJ 

$WR *** OBJECT OF OS @1.0BJ MISSING *** 

$CLEAR 

$ENDC 

$BUILD @1.LNK 

NLOG 

ESTAB OS 

INCL @1.0BJ 

$ENDB 

SYSCHECK @1,USERDLIB.LIB,1 

SYSCHECK ©l^SERSYS.LIB,! 

SYSCHECK @1,@2DRIVER.LIB 

SYSCHECK @1,@2SYS.LIB 

SYSCHECK @1 / @2ITBDLIB.LIB,1 

SYSCHECK @1,@2ITBSYS.LIB 

SYSCHECK @1 / @2ITES2780.LIB,1 

SYSCHECK @1,@2ITED2780.LIB,1 

SYSCHECK @1,@2ITEDZDLC.LIB,1 

SYSCHECK @1,@2ITESZDLC.LIB / 1 

♦SYSCHECK @1,ITED327S.LIB,1 

*SYSCHECK @1,ITED327E.LIB / 1 

SYSCHECK @l / @2UBOT.OBJ 

$BUILD @1.LNK / APPEND 

MAP @1.LST,ADDR, ALPHA 

BUILD @1.0S 

END 

$ENDB 

XDE @1.0S 
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LO . BG, LINK. TSK/S, 100; TA . BG 

ST , C0MM=@1 . LNK , LOG=NULL : 

$IFNE O; $WR *** LINK ERROR ***; $CLEAR; $ENDC 

$IFNULL @3 

XDE @1.LNK;$ENDC 

$WR OS MAP ==> @1.LST 

$WR OS OBJ ==> @1.0BJ 

$WR OS TSK ==> @1.0S 

$EXIT 

* 

3.5 CUPMT VS. SYSGEN/32 

It is appropriate to introduce here a discussion of the major differences between CUPMT and 
SYSGEN/32. The differences lie in the specification of a shared busy condition and specification 
of controllers without specific device addresses. 

A shared busy condition (a common leaf) must exist if a device shares the same address as 
another device. (This is not necessarily true for pseudo-devices.) When generating a system with 
CUPMT, this condition was specified explicitly by an asterisk as the control number, in column 
1 of the device(s) sharing the busy condition. With Sysgen/32, the shared busy condition is set 
automatically by the program if the device address specifications are the same. 

Under CUPMT, a shared busy condition must be explicitly declared: 

3 D80F:FC,62,D 
* D16R:FC,59,D 

Under CUPMT, controllers are on separate SELCHs: 

1:F0,0 

2:0,0 specify the controller as zero 

3 MAGI: 85, 65 

1:F1,0 

2:0,0 specify the controller as zero 

3 MAG2:C5,65 

Under Sysgen/32, a shared busy condition is generated automatically when the same address is 
specified: 

D80F : , FC, 62 , SELCH=F0, C0NTR=FB 
D16R: , FC, 59, SELCH=F0, C0NTR=FB 

In addition, under SYSGEN32 controllers are on separate SELCHs: 

MAGI : , 85, 65, SELCH=F0, C0NTR=0 
MAG2 : , C5 , 65 , SELCH=F1 , C0NTR=1 
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CHAPTER 4 
SAMPLE DRIVERS 

4.1 INTRODUCTION 1 

4.2 SAMPLE DRIVER FOR DIGITAL INPUT/OUTPUT (DIO) INTERFACE 1 

4.3 TELEX TRIDENSITY MAGNETIC TAPE DRIVER 8 



CHAPTER 4 



SAMPLE DRIVERS 



4.1 INTRODUCTION 

This chapter provides two sample drivers as models. The first, a digital input/output (DIO) driver, 
is a very simple and typical driver. The other sample driver, a TELEX tridensity tape driver, is a 
complex driver containing many of the possible features that can be found in a driver. 

4.2 SAMPLE DRIVER FOR DIGITAL INPUT/OUTPUT (DIO) INTERFACE 

The driver for DIO is a typical driver needed by users seeking an interface with the operating 
system. It is a very simple driver written under a selector channel (SELCH), and it provides an 
interface in a situation where the configuration is unlike the one supported by the standard Perkin- 
Elmer driver. In this driver, starting in column 73, a description of the code, i.e., the driver 
initialization routine (DIR), interrupt service routine (ISR), event service routine (ESR) and I/O 
handlers (IOH), is provided. Where more than one of these routines occur, a sequence code (1-9, or 
a-z) follows the basic description. 



BASIC DRIVER LOGIC - CASE 7 

THE FOLLOWING DRIVER IS PROVIDED TO 
RELATIVELY STRAIGHT FORWARD DIO DEVICE 



ILLUSTRATE PROGRAMMING OF A 



BATCH 



**SDIO 



MLIBS 8,9,10,11 
SDIO $DVPR0G TAL 1/0,05, 07-083 $REGS$ 

$DCB$ 

$CCB 

$TCB 

ENTRY INITSDIO,TERMSDIO 

EXTRN IODONE,SQ,ISPTAB,DIRDONE,III 

EXTRN T0CH0N,T0CH0FF 

TITLE INITIATION PHASE FOR DIGITAL I/O 
* INITSDIO EQU * 

LHI U1,X'8600' 

L U6,DCB.SADR(UD) 

THI U6,l 

BNZ SDIOSTAT 

LHI U^X'COOO' 

LH U9,DCB.DN(UD) 

LH UA,DCB.FC(UD) 



POSSIBLE ERROR CODE: SET UP 

GET START ADDRESS 

IS IT ON HW BOUNDARY? 

NO, ERROR 

POSSIBLE ERROR CODE: SET UP 

GET DEVICE ADDRESS 

GET FUNCTION CODE 



structs 
structs 
structs 
entrys 

extrns 
extrns 



dir 
dlr 
dir 
dir 
dir 
dir 
dir 
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THI 
BNZ 
THI 
BNZ 
B 

SDI OREAD EQU 
THI 
BZ 

SDIOCOM EQU 
LH 
LHI 
OC 
BTC 
LHI 
STH 
LIS 
STH 
BAL 
LHL 
LA 
STH 
LA 
LH 
STH 
LH 
SINT 
B 
ALIGN 

STOPSEL DC 

ALIGN 

SDIOSTAT EQU 
LIS 
ST 
STH 
B 

* 



UA,X'4000' 

SDI OREAD 

U9,l 

SDIOSTAT 

SDIOCOM 

* 

U9,l 
SDIOSTAT 

* 

UB,DCB.SDN(UD) 

Ul,X'AOOO* 

UB, STOPSEL 

4, SDIOSTAT 

U2,X'7FFF' 

U2, DCB. TOUT (UD) 

U2,0 

U2 , DCB . STAT (UD) 

U8,T0CH0N 

UCDCB.CCB(UD) 

U2,ISRSDIO 

U2,CCB.SUBA(UC) 

U2,1(UC) 

UB,DCB.SDN(UD) 

U2,ISPTAB(UB,UB) 

U8,DCB.ILVL(UD) 

U8,0(UB) 

DIRDONE 

2 

X ' 4800 ' 

4 

* 

U2,0 

U2,DCB.LLXF (UD) 
Ul, DCB. STAT (UD) 
IODONE 



* TRANSFER INITIATION INTERRUPT 



ISRSDIO 



PURE 

EQU 

L 

THI 

BNZ 



IS IT A READ? 
YES, BRANCH 
IS DEV ADDR ODD? 
YES, ERROR 



IS DEV ADDR EVEN? 
YES, ERROR 

GET SELCH ADDRESS 

POSSIBLE ERROR CODE: SET UP 

RESET THE SELCH 

IF FALSE SYNC, ISSUE D.U. STAT 

SET TIME OUT TO 'DON'T CARE' 

* UNTIL ISR IS STARTED 

CLEAR DEV STAT - WE WILL USE THIS 

* AS A FLAG BETWEEN ISR AND ESR. 
GO GET ON TIMER CHAIN. 

GET CCB 

ISR RETURN ADDRESS 

PUT IN CCB 

GET CCB ADDR + 1 

GET SELCH ADDRESS 

PUT IN ISPTAB 

GET INTERRUPT LEVEL 

FIRE UP SELCH 



ZERO LLXF 
STORE IN STATUS 
QUIT 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 



E5,CCB.DCB(E4) 

E3,X'34' 

FALSYNC 



GET DCB ADDRESSS 
CHECK STATUS ON SELCH 
DEVICE UNAVAILABLE 



err 
err 
err 
err 
err 



isrl 
isrl 
isrl 
isrl 
isrl 
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LH E6,DCB.DN(E5) 

OC E6,X80 

BTC 4,FALSYNC 

OC E2,STOPSLCH 

WD E2,DCB.SADR+1(E5) 

WH E2,DCB.SADR+2 (E5) 

WD E2,DCB.EADR+1(E5) 

WH E2,DCB.EADR+2(E5) 

LA E3,ISR1SDI0 

STH E3,CCB.SUBA(E4) 

LIS E3,5 

STH E3,DCB.T0UT(E5) 



E7,DCB.FC(E5) 

E7,X'4000* 

ISRSELRD 

E6,X00 

E2,SELCHWRT 



LH 
THI 
BNZ 
WH 
OC 

LPSWR EO 
ISRSELRD EQU * 

RHR E6,E7 

OC E2,SELCHRD 

LPSWR EO 



GET DEVICE NUMBER 

DISABLE INTERRUPTS FROM DIO 

IF DIO GIVES FALSE SYNC, EXIT NOW 

WE ARE NOW COMMITTED TO DOING THE 

* TRANSFER, SO GET THE START AND 

* END ADDRESSES WRITTEN TO THE SELCH 

* 

ISR RETURN ADDRESS 
SET 5 SECOND TIMEOUT. 



GET FUNCTION CODE 
IS IT A READ? 
YES, BRANCH 
PRIME OUTPUT DEVICE 
START SELCH 



PRIME INPUT DEVICE 
START SELCH 



isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 



FALSYNC 



EQU 

LHI 

STH 

B 

DC 

DC 



E6,X'A000' 

E6,DCB.STAT(E5) 

ISRDSARM 

X ' 8000 ' 

X * 0000 ' 

X'14' 

X'34' 

X*48' 

4 



X80 
XOO 

SELCHWRT DB 
SELCHRD DB 
STOPSLCH DB 

ALIGN 

* 

* OPERATION COMPLETE INTERRUPT. 
* 

* 

E5,CCB.DCB(E4) 

E3,X'34' 

ISRDSARM 

E7,X'8400' 

E7,DCB.STAT(E5) 



ISR1SDI0 EQU 
L 

THI 
BZ 
LHI 
STH 



DEVICE UNAVAILABLE 
SAVE IN STATUS 



GET DCB ADDRESS 
BAD STATUS ON SELCH? 
IF NO PROBLEM, GO ON 
UNRECOVERABLE ERROR 



isr2 
isr2 
isr2 
isr2 



isr2 
isr2 
isr2 
isr2 
isr2 
isr2 
isr2 
isr2 
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ISRDSARM 


EQU 


* 




LA 


E3, III 




STH 


E3,ISPTAB(E2,E2) 




LHI 


E3,Y'7FFF' 




LH 


E7,DCB.T0UT(E5) 




STH 


E3,DCB.T0UT(E5) 




BZ 


ISRRTN 




L 


E7,DCB.LEAF(E5) 




ATL 


E7,SQ 




LPSWR 


EO 


ISRRTN 


EQU 


* 




LHI 


E3,X'8298' 




STH 


E3,DCB.STAT(E5) 


* 


LPSWR 


EO 


* EVENT 

* 


SERVICE ROUTINE. 




IMPUR 




TERMSDIO 


EQU 


* 




LH 


U9,DCB.STAT(UD) 




BNZ 


XFERERR 




LH 


U9,DCB.SDN(UD) 




OC 


U9,ST0PSEL 




RDR 


U9,UA 




RHR 


U9,UB 




SLL 


UA,16 




OR 


UA,UB 




C 


UA,DCB.EADR(UD) 




BP 


SLCHFAIL 




S 


UA,DCB.SADR(UD) 




BM 


SLCHFAIL 




AIS 


UA, 1 




ST 


UA,DCB.LLXF(UD) 




LH 


U8,DCB.T0UT(UD) 




BNZ 


TDIOCHOE 




LHI 


U6,X'8298' 




STH 


U6,DCB.STAT(UD) 


TDIOCHOE 


■ EQU 


* 




BAL 


U8 , TOCHOFF 


* 


B 


IODONE 


XFERERR 


EQU 


* 




LIS 


UO,0 



RESET THE INTERRUPT VECTOR 

* SO THAT THERE WILL BE NO STRAY 

THIS WILL RESET TIMEOUT VALUE 

DID WE TIME OUT? 

CLEAR TIMEOUT COUNTER 

YES, DON'T SCHEDULE TERM 

PUT LEAF ADDRESS ON SYSTEM QUEUE 
AND EXIT ISR 

SET TIMEOUT ERROR CODE 



DID WE GET AN ERROR? 
IF SO, DO SPECIAL STUFF. 
GET SELCH ADDRESS 

STOP SELCH, EXTENDED ADDRESS READ 
READ SELCH FINAL ADDRESS 
( ALL 3 BYTES ) 

MAKE A 24 BIT WORD OUT OF THIS 
GOT FINAL SELCH ADDRESS NOW. 
DID IT EXCEED SPECIFIED FINAL? 
IF SO, EXIT. 

CALCULATE LENGTH OF TRANSFER 
IF WE WENT BACKWARDS - FAILED. 
ARITHMETIC ADJUSTMENT 
GIVE USER LENGTH OF TRANSFER. 
TIMED OUT? 
NO, BRANCH 
UNRECOVERABLE ERROR 



REMOVE FROM TIMER CHAIN 
WE'RE THROUGH 



CLEAR LENGTH OF TRANSFER 



isr2 

isr2 

isr2 

lsr2 

isr2 

isr2 

isr2 

isr2 

isr2 

isr2 

timeout 

timeout 

timeout 

timeout 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

esr 

err 
err 
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ST 


UO,DCB.LLXF(UD) 


* 


err 


LHI 


U0,X*7FFF' 


RESET TIME-OUT VALUE TO DONT CARE. 


err 


STH 


UO,DCB.TOUT(UD) 


* 


err 


BAL 


U8 , TOCHOFF 


GET OFF TIMER CHAIN 


err 


B 


IODONE 




err 


SLCHFAIL EQU 


* 




err 


LHI 


UCX^OOO' 


INDICATE EOM ON SELCH 


err 


STH 


UO, DCB. STAT (UD) 




err 


B 


XFERERR 


* 


err 


END 









The following device control block (DCB) shows the code required to write a DCB when using 
CUPMT to generate the system. The DCB and channel control block (CCB) macros may be found 
in SYSSTRUC.MLB. These macros are also listed in Appendix C of Part II of this manual. 

**DCB143 

MLIBS 8,9,10 

NLIST 

DPROG DC0D=143 

LIST 
EXTRN Z (CDN1) 
* 

* BUILD DCB FOR DIGITAL I/O DRIVER 

* 

DCB DC0D=143,INIT=INITSDI0,TERM=TERMSDI0, 1 

ATRB=7F00,RECL=0,SIZE=DCB.DVDP+8, 1 

FLGS=DFLG.LNM 



INITIAL VALUE 



DCB.IVAL EQU DCB.RTRY 




ORG DCB143+DCB. 


,IVAL 


DC H'O' 




* DEVICE DEPENDENT PART 




ORG DCB143+DCB. 


,CCB 


DC Z (CCB143) 




DC X ' ' 




ORG DCB143+DCB.SDN 




DC Z (CDN1) 
* 




* BUILD CCB FOR DIGITAL 

* 


I/O : 


CCB DC0D=143 




NLIST 




END 




BEND 





CCB 
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The following macro shows the DCB specification for the DIO driver when using Sysgen/32 for 
sysgen. Note that the DCB specification is a separate macro file and is NOT a part of the driver (as 
is the case in a CUPMT system). The DCBI and CCBI macros can be found in SYSGEN32.MLB. 
These macros are also listed in Appendix C of Part II of this manual. 

MACRO 

DCB242 %DCOD=,%DN=,%CLAS=,%ILVL=,%NAME=,%SHCCB=, 1 

%SLCH=,%CNTR= 

GBLB %DCB$ , %PDCB , %DDCB , %E VN , %CCB , %DFLG , %SDCB 

GBLB %IDCB,%ODCB,%S125DCB,%ICCB,%BDCB 

GBLB %ADCB , %TCB , %I OB ( %I 0B$ , %CRTDCB , %LPDCB 

GBLB %MMDDX , %DDEX , %VFDCB , %MTP , %CRPDCB , %MGDCBX , %HFWDST 

GBLB %PSDCBX, %CRDP , %AOBDCB, %BIOCDCB, %LPTDCB 

GBLB %C0RD242 

GBLC %IDVAL 

BGBLA %ID242 

LCLA %CCBFL 

LCLA %CLASN 

LCLC %RXLT,%RQU 

LCLC %CORDNM,%PTRPAS 

LCLC %OFFS 

LCLA %RDN 

LCLC %MDN , %MCNT , %MSLCH 

LCLA %TRCNT , %UPTR 

LCLB %FOUND / %DA 

BGBLA %FIRST 
%RQU SETC 'COMQ' DEFAULT DEVICE QHANDLER 

%MDN SETC '%DN' DEVICE ADDRESS 

%CCBEL SETA 
%C0RD242 SETB 

AIF (T'%CLAS EQ 'U*)&CLSNTD 
%CLASN SETA %CLAS*12 I0CLASS*12 

&CLSNTD ANOP 

CONVNUM VAL=%ID242 CONVERT CURRENT ID TO HEX. 

USERINIT 

$DCB$ 

DCBI DC0D=242,SIZE=DCB.DVDP+8,INIT=INITSDI0, 1 

TERM=TERMSDIO,FLGS=DFLG.LNM / 2 

ID=%IDVAL , ATRB=7F00 

CCBI DCOD=242, ID=%IDVAL / SUBA=III 
CCB%NAME EQU CCB%DCOD%IDVAL 
%ID242 SETA %ID242+1 
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&DCBOPT ANOP 
DCB%DCOD%IDVAL 
%OFFS SETC 
DCB.%NAME EQU 



PROG USER DCB 
'%DCOD' : '%IDVAL* 
DCB%OFFS 



ESTABLISH PROPER OFFSET 



ENTRY DCB.%NAME 
ORG DCB%OFFS+DCB.DMT 
DC DMT.%NAME 
EXTRN DMT.%NAME 



ORG 


DCB%OFFS+DCB.DN 


DC 


H ' %DN * 


DCB.IVAL EQU 


DCB.RTRY 


ORG 


DCB%OFFS+DCB. IVAL 


DC 


H'O' 


ORG 


DCB%OFFS+DCB . LEAF 


AIF 


(T'%SHCCB' EQ 'U' 


DAC 


LF%SHCCB 



DEVICE ADDRESS 



&NSLEAF 



&NRMLFX 
&NOLEAF 



&NOCLAS 



&NOILVL 



&NOQU 



&NSLCH 



LEAF POINTER 
SLEAF B IF NOT SHARED 

USE SHARED DEVICE LEAF 
EXTRN LF%SHCCB 
AGO &NRMLFX 
ANOP 

DAC LF%OFFS GENERATE STANDARD LEAF NAME 

EXTRN LF%OFFS 
ANOP 
ANOP 
AIF 
ORG 
DC 

ANOP 
AIF 
ORG 
DC 

ANOP 
AIF 
ORG 
DAC 



(T'%CLAS EQ 'U')&NOCLAS 
DCB%OFFS+DCB.CLAS 10 CLASS 
H'%CLASN' I0CLASS*12 

(T'%ILVL EQ 'U'J&NOILVL 
DCB%OFFS+DCB.ILVL ILEVEL 
H*%ILVL* 

('%RQU' EQ ")&NOQU 
DCB%OFFS+DCB.Q 
%RQU 



EXTRN %RQU 
ANOP 



AIF 

ORG 

DC 

ANOP 

AIF 

ORG 

DC 



(*%SLCH' EQ 'U')&NSLCH 
DCB%OFFS+DCB.SDN 
X'%SLCH' 

(^CNTR" EQ 'U'J&NCNTR 
DCB%OFFS+DCB.CDN 
X'%CNTR' 
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&NCNTR 


ANOP 






ORG 


$ST%OFFS 




ASIS 






END 




%RDN 


SETA 
MEND 


%DN+1 



ORG TO END OF DCB 



4.3 TELEX TRIDENSITY MAGNETIC TAPE DRIVER 

This sample driver, a TELEX magnetic tape driver, was written to accommodate a modified 
Perkin-Elmer 35-820 tape interface. This includes special device-dependent functions, such as 
erase gap, rewind and unload, and read status. (Tridensity refers to the fact that it operates on 
three different recording densities.) This driver, as opposed to the previous one, is a very complex 
driver and was chosen as an example because it contains so many of the features that a driver is 
capable of having. For example, a TELEX driver contains retry logic, multiple ESRs, and 
supervisor call 1 (SVC1) command function processing. It also contains resource releases, a 
mechanism by which you can release a particular resource (e.g., SELCH or controller) into the 
system . 

Note that in this type of driver, the ISR (PURE) code is put immediately after the DIR or 
ESR that enters the ISR via a SINT. Similarly, the ESR code immediately follows the ISR that 
schedules it. This is done to allow the reader to more easily follow the logic flow through the 
driver. Also note that generally, in the case of conditional branches, the normal logic path is to 
NOT take the branch. This is important because the driver is then easier to read and the 
execution speed on the Model 3240/3250 processors is improved. 

Of further interest is the fact that this driver happens to contain some sense status loops. This is not 
normal practice in writing drivers and should be avoided whenever possible. The loops in this 
driver were included after experimentally determining that the no-motion status bit was set after 
a minimal amount of time, i.e., after a minimal number of times through the loop. Otherwise, if 
the no-motion status bit is not set right away, the status loop is monopolizing too much of the 
processor's time, and it is preferable to set up an interrupt, which is the normal programming 
practice in writing drivers. In this particular case, the status loop was necessary. 
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USED BY $MTP MACRO 
TELEX MAG TAPE DRIVER 



BATCH 

LCNT 50 

MLIBS 8,9,10 
SGN . EOV EQU 1 
INITTELX PROG 

NLIST 

$UREGS 

$EREGS 

$PSW 

$SVC1 

$SVC7 

$EVN 

$IOH 

$DCB$ 

$CCB 

$TCB 

$T0PT 

$MTP 

LIST 

TITLE ENTRY'S, EXTRN * S & EQUATES 

ENTRY INITTELX, CMDTELX,TERMTELX 

EXTRN ADCHKNS , DMT , EVREL , EVRTE , I I I , I ODONE , I SPTAB 

EXTRN MEMFAULT,RELIOB, SQ, SV9 .ATQ1 

EXTRN SVC1BFM, SVC1BSR, SVC1DDF , SVC1FFM, SVC1FSR, SVC1HALT 

EXTRN SVC1N00P , SVC1READ, SVC1REW, SVC1TEST, SVC1WAIT 

EXTRN SVC1WFM, SVC1WRIT, TOCHOFF , TOCHON, UBOT 

SPACE 

* STATUS BYTE DEFINITION. 
* 

* THE FOLLOWING STATUS INFORMATION MAY ALSO BE FOUND IN 

* THE PERKIN-ELMER HIGH PERFORMANCE TAPE DRIVE (HPTD) 
CONTROLLER INSTALLATION AND MAINTENANCE MANUAL. 
PUBLICATION NUMBER (47-028R00) . 



strucs 
strucs 
strucs 
strucs 
strucs 
strucs 
strucs 
strucs 
strucs 
strucs 
strucs 
strucs 



THE CONTROLLER STATUS BYTE IS OBTAINED BY USE OF THE 
SENSE STATUS OR SENSE STATUS REGISTER INSTRUCTIONS. 



ERR 

TERR 

EOM 

NMTN 

BSY 

EX 



EQU 
EQU 
EQU 
EQU 
EQU 
EQU 



X'80' 
X'40' 
X'20' 
X'lO' 
X'08* 
X'04' 



ERROR STATUS 
TRANSFER ERROR STATUS 
END OF TAPE STATUS 
NO MOTION STATUS 
BUSY STATUS 
EXAMINE STATUS 
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EOF EQU X'02' TAPE MARK STATUS (END -OF -FILE) 

DU EQU X'Ol' DEVICE UNAVAILABLE STATUS 

TAPELTH EQU 28800 MAXIMUM TAPE LENGTH 
* 

* THERE ARE TWO METHODS OTHER THAN A SENSE STATUS ON THE 

* CONTROLLER, TO OBTAIN REQUIRED INFORMATION ABOUT A TELEX 

* TAPE UNIT. 

* 

* NO-OP COMMAND. 
* 

* THE NO-OP COMMAND RETURNS DEVICE STATUS HALFWORD INFORMATION. 

* THERE ARE FOUR POSSIBLE HALFWORDS THAT MAY BE READ. ONLY 

* THE READ STATUS COMMAND RETURNS ALL FOUR TO THE USER. THE 

* DRIVER USES THE NO-OP COMMAND TO DETERMINE THE DENSITY OF 

* THE DRIVES (REQUIRED FOR APPROPRIATE TIMEOUT CALCULATIONS) . 
* 

* UPPER HALFWORD IS THE SAME FOR ALL 4 DEVICE STATUS HALFWORDS. 
* 

* BIT 8 - ZERO. 

* BITS 9 & 10 - DENSITY 

* BIT 9 BIT 10 

* 10 NRZI 

* PE 

* 1 GCR 

* BIT 11 - BLOCK (SET WHEN BLOCK STATUS DETECTED FROM FCU) 

* BIT 12 - ODDBYTE (SET WHEN TRANSFER ENDS ON ODD-BYTE BOUNDARY) 

* BIT 13 - WRITE UNDERFLOW 

* BIT 14 - BUS PARITY 

* BIT 15 - READ OVERRUN 
* 

* 

* SENSE COMMAND (X'30') 
* 

* SENSE BYTE O 

* BIT O - LOAD POINT... SET WHEN THE TAPE UNIT IS AT LOAD POINT. 

* BIT 1 - FILE PROTECT. SET WHEN TAPE UNIT IS WRITE PROTECTED. 

* BIT 2 - BACKWARD STATUS. SET WHEN TAPE UNIT IS PERFORMING OR 

* HAS PERFORMED A BACKWARD OPERATION. 

* BIT 3 - WRITE STATUS. . .TAPE UNIT IS NOT IN READ MODE. 

* BIT 4 - EOT.. SET WHEN LEADING EDGE OF EOT MARKER IS SENSED 

* DURING A FORWARD OPERATION AND RESET WHEN THE 

* TRMLING EDGE OF EOT MARKER IS SENSED DURING 

* A BACKWARD OPERATION. 
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* BIT 5 - LO DENSITY. . .SET WHEN A DUAL DENSITY TAPE UNIT IS 

* OPERATING IN THE LOWER DENSITY MODE. 

* BIT 6 - READY. . .SET WHEN A TAPE IS LOADED AND THE TAPE UNIT 

* IS ON-LINE. 

* BIT 7 - COMMAND REJECT.. SET IS THE COMMAND BYTE HAS EVEN 

* PARITY OF IF A WRITE COMMAND IS RECEIVED IN 

* CONJUCTION WITH A BACKWARD MOTION COMMAND. 
* 

* 

TITLE SPECIAL STATUS DEFINITIONS 
* 

* FOR EASE OF DEBUGGING BOTH SOFTWARE AND HARDWARE RELATED 

* PROBLEMS, THIS DRIVER REPORTS AS MUCH UNIQUE STATUS INFORMATION 

* AS IS POSSIBLE WITHOUT CONFLICTING WITH THE NORMAL (EXPECTED) 

* STATUS SUCH AS EOF, AND EOT. 
* 

* 

* X'8241' - TIME-OUT ON READ DEVICE HALFWORD ISSUED AT THE 

* START OF THE DRIVER TO OBTAIN DENSITY. NO-MOTION 

* DID NOT SET AFTER A LOOP COUNT OF 63. 

* X'8282* - TIME-OUT ON A WRITE OPERATION. 

* X'8263' - TIME-OUT ON A READ OPERATION. 

* X'8484' - SELCH FINAL ADDRESS WAS LESS THAN START ADDR (READ/WRITE) 

* X'8271' - TIME-OUT ON FORWARD/BACKSPACE RECORD. 

* X*8275' - TIME-OUT ON WRITE FILEMARK. 

* X'8272' - TIME-OUT ON FORWARD/BACKFILE OPERATIONS. 

* X'8273' - TIME-OUT ON ERASE GAP FUNCTION. 

* X'82DD' - TIME-OUT ON READ STATUS FUNCTION. 

* X'82DE' - TIME-OUT ON READ DEVICE HALFWORD ISSUED TO 

* CHECK FOR WRITE PROTECT CONDITION. 

* X'82DF' - TIME-OUT ON READ DEVICE HALFWORD ISSUED TO 

* CHECK FOR EOT/BOT CONDITIONS. 

* X'8283' - WRITE PROTECT INDICATOR. 

* X'8277' - TIME-OUT ON REWIND FUNCTION. 

* X'AOOO' - DEVICE UNAVAILABLE. 

* X'9000' - END OF TAPE. 

* X'8400' - UNRECOVERABLE ERROR (ERR OR TERR BUT NOT NO-MOTION). 

* X'82FA' - PARITY ERROR (TRUE PARITY) OR ATTEMPT TO 

* READ LESS THAN A FULL RECORD ON NON-EXTENDED 

* OPTION I/O. 

* X'82AA* - FILE MARK ERROR - OCCURS WHEN READING LARGE 

* AREAS OF ERASED TAPE. AS LONG AS THIS STATUS 

* OCCURS THE USER SHOULD FORWARD SPACE RECORD TO 
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GET BY THE ERASE AREA. (THIS STATUS OCCURS 
AFTER 10 FEET OF ERASED TAPE, WHICH IS AS MUCH 
AS THE FORMATTER WILL MOVE THE TAPE WITHOUT 
EXPECTING A FILE MARK IN THE ERASED AREA) . 



* CRASH CODES GENERATED WITHIN THIS MODULE. 

* CRASH 502 - OCCURS WHEN THE SELCH FINAL ADDRESS IS LESS 

* THAN THE SELCH START ADDRESS AND THE FINAL 

* ADDRESS IS LESS THAN UBOT (THIS MEANS O.S 

* CODE WAS OVERWRITTEN) . 



* REGISTER CONVENTIONS 



* (REGISTER SET 5 ) 

* UO - SCRATCH 

* Ul - SCRATCH 

* U2 - SCRATCH 

* U3 - SCRATCH 

* U4 - SCRATCH 

* U5 - SCRATCH 

* U6 - DEVICE ADDRESS 

* U7 - SCRATCH 

* U8 - SCRATCH 

* U9 - SCRATCH 

* UA - SCRATCH 

* UB - SCRATCH 

* UC - CCB ADDRESS 

* UD - DCB ADDRESS 

* UE - SCRATCH 

* UF - LEAF ADDRESS BEFORE CALL TO EVREL 

TITLE DRIVER INITIALIZATION 
INITTELX EQU * 



CMDTELX 


EQU 


* 


TLX0010 


EQU 


* 




LHL 


UCDCB.CCB(UD) 




LHL 


U6,DCB.DN(UD) 




LH 


U7,DCB.SDN(UD) 




OC 


U7 , CLEARSEL 




LHL 


U8,DCB.FLG1(UD) 




SSR 


U6,U7 




BTC 


5,TLX2250 



ALSO EQUAL TO INITMAG 

SET UP CCB POINTER 

GET DEVICE ADDRESS 

GET SELCH ADDRESS 

CLEAR SELCH 

GET THE FLAGS 

GET THE DRIVE STATUS 

IF EX OR DU, DO EXTRA CHECKS 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
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TLX0015 EQU * 

THI U7, ERR! TERR! NMTN 

BZ TLX2260 

THI U7 , NMTN 

BZ TLX2350 

TLX0018 EQU * 

OC U6,DCB.CCLC(UD) 

LA U9 , TLX0020 

THI U8,X'0800' 

BNZ TLX2050 

THI U7 , EOM 

BNZ TLX2050 

NHI U8,X'33FF' 

STH U8 , DCB . FLG1 (UD) 

TLX0020 LIS UO,0 

STH UO , DCB . STAT (UD) 



RETURN HERE FROM MORE CHECKING 

IF NONE OF THESE ARE SET, 

WE ASSUME IT IS REWINDING: BRANCH 

IF ERR OR TERR AND NOT NMTN, 

EXIT WITH X'8400 1 STATUS. 

START HERE AFTER REWIND FINISHES 

CLEAR CONTROLLER 

SET EOT/BOT CHECK RETURN 

WAS EOT PREVIOUSLY ENCOUNTERED 

IF SO, MUST GO DO FULL CHECK 

ARE WE NOW AT END OF TAPE? 

YES, GO DO FULL CHECK 

RESET BITS 0,1,4,5 

SAVE THE FLAGS 

CLEAR STATUS BEFORE WE START 



GET THE DENSITY SELECTION OF THE TRANSPORT UNIT. 

FROM THIS INFORMATION, COMPUTE THE DATA TRANSFER RATE, 

ASSUMING THAT THE DRIVE OPERATES AT 125 IPS. 



OC U6,DCB.DSB0(UD) 

LHI Ul,63 

TLX0030 SIS Ul,l 

BNP TLX0055 

SSR U6,U2 

THI U2,X'10' 

BZ TLX0030 

TLX0040 RHR U6 , U2 

NHI U2 , X ' 60 * 

SRLS U2 , 3 

L U1,DCB.XRT(UD,U2) 

ST 



GIVE FORMATTER A NO-OP CMD 

SET LOOP COUNT - PREVENT HANGS! 

DECR THE LOOP COUNT 

COUNTED OUT - TIME OUT THIS OP. 

GET STATUS 

DID NO-MOTION SET? 

IF NOT, LOOP UNTIL IT IS SET 

GET THE DEVICE STATUS H/W 

MASK DENSITY BITS 

MAKE FULL WORD INDEX 

GET ACTUAL TRANSFER RATE 

AND SAVE FOR LATER USE 



Ul, DCB. RATE (UD) 
NOTE - U2 MUST BE PRESERVED IF THE REQUEST IS AN 
•ERASE BUFFER' DEVICE -DEPENDENT COMMAND FUNCTION. 

COMPUTE THE REQUESTED LENGTH OE TRANSFER. 

L U9 , DCB . EADR (UD) GET END ADDRESS 
S U9,DCB.SADR(UD) LESS THE START ADDRESS 
AIS U9,l ADJUST FOR INCLUSIVE ADDRS 

ST U9,CCB.XLT(UC) SAVE FOR LATER REFERENCE 



* U9 WILL BE USED A LITTLE LATER 



DO NOT DESTROY! 



dlr 
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dir 
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* IF THE SVC 1 FUNCTION CODE INDICATES A COMMAND FUNCTION, 

* BRANCH TO DETERMINE WHAT FUNCTION TO PERFORM. 



LB U3,DCB.FC(UD) 
THI U3 , X ' 80 ' 
BP TLX1280 



GET SVC 1 CODE 

CHECK FOR COMMAND BIT ON 



* IF THE TASK IS NOT LINKED WITH EXTENDED SVC1 OPTION, FORCE 

* THE EXTENDED SVC 1 FUNCTION FIELD TO ZERO FOR LATER USE. 

* THEN DETERMINE WHICH ROUTINE TO GO TO, BASED ON THE 

* EXTENDED FUNCTION CODE AND BITS 1 AND 2 IN THE STANDARD 

* SVC 1 FUNCTION FIELD. 



LI 


U0,T0PT.X1B 


L 


U1,DCB.TCB(UD) 


TBT 


U0,TCB.0PT(U1) 


BZ 


TLX0070 


L 


U1,DCB.SV1X(UD) 


NI 


U^X'IF' 


SLLS 


Ul,2 


L 


U1,TLX0050(U1) 


BR 


Ul 



FURTHER CHECK FOR TASK OPTION 

GET TCB ADDRESS 

GET TASK OPTION FIELD 

NOT LINKED WITH EXTENDED OPTRWNS 

FETCH USER EXTEND OPTION 

EXTRACT THE EXTEND CODE 

INDEX INTO TABLE FOR EXEC ROUTINE 



SPACE 1 



ALIGN 


4 




TLX0050 EQU 


* 




DAC 


A (TLX0080) 





DAC 


A (TLX0080) 


1 


DAC 


A(TLX0060) 


2 


DAC 


A(TLX0060) 


3 


DAC 


A(TLX0080) 


4 


DAC 


A(TLX0080) 


5 


DAC 


A(TLX0080) 


6 


DAC 


A(TLX0080) 


7 


DAC 


A (TLX0080) 


8 


DAC 


A(TLX0080) 


9 


DO 


22 




DAC 


A(TLX2360) 




SPACE 


1 





COME HERE ONLY ON TIME-OUT OF READ DEVICE STATUS HALFWORD 
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TLX0055 EQU 
LHI 
STH 
B 

TLX0060 EQU 
BAL 
B 

TLX0070 EQU 
LIS 
ST 

TLX0080 EQU 



U8,X'8241' 

U8,DCB.STAT(UD) 

TLX2150 
* 

UB,TLX1940 
TLX0920 

U1,0 
U1,DCB.SV1X(UD) 



SET A TIME-OUT STATUS 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 

IF FILE PROTECT NO RETURN 



RESET EXTENDED OPTIONS FIELD 



U3 = SVC 1 FUNCTION CODE FIELD. 



IF THE REQUESTED LENGTH IS LESS THAN 4, EXIT 



CHI 
BL 



U9,4 
TLX2360 



TOO SHORT (LESS THAN 4 BYTES) 
IF SO, EXIT WITH ILLEGAL FNCTN 



CALCULATE THE APPROPRIATE TIME-OUT VALUE, BASED ON 
THE DENSITY SETTING READ FROM THE FORMATTER. 





LIS 


Ul,l 




L 


UO,CCB.XLT(UC) 


TLX0085 


AIS 


Ul,l 




S 


UO,DCB.RATE (UD) 




BP 


TLX0085 


* 


STH 


Ul,CCB.LBO(UC) 




THI 


U3,SV1.READ 




BNZ 


TLX0320 




THI 


U3,SV1.WRIT 




BZ 


TLX2360 




BAL 


UB,TLX1940 



SET UP TO CALCULATE TIME-OUT 

GET COMPUTED XFER LENGTH 

ADD 1 SECOND FOR EACH RATE SIZE 

COMPARE SIZE TO RATE 

LOOP UNTIL SIZE FIELD IS COUNTED 

SAVE TIME-OUT TEMPORARILY 

READ? 

YES, GO READ ONE RECORD 

WRITE? 

NO, ILLEGAL FUNCTION 

IF FILE PROTECT NO RETURN 



TITLE WRITE OPERATIONS 
******************** 

* WRITE ONE RECORD 
* 

* SET UP RETRY COUNTERS 
* 



LIS UO,0 

STH UO , DCB . RTRY ( UD ) 



INITIALIZE RETRY 
COUNTER 
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LH U1,DCB.WRY1(UD) 

L U0,DCB.SV1X(UD) 

BZ TLX0090 

LB U1,DCB.SV1X(UD) 

TLX0090 STH Ul, DCB.RMAX (UD) 

L U2,CCB.XLT(UC) 

THI U2 , 1 

BZ TLX0120 

LI U1,MAGHLFB 

SBT U1,DCB.FLG1(UD) 



GET DEFAULT WRITE RETRY COUNT 

GET EXTENDED FUNCTION CODE 

IF EXT. FNCTN = 0, USE DEFAULT 

IF NOT, USE USER'S COUNT 

SET RETRY COUNT. 

GET REQUESTED LENGTH OF XFER 

ODD BYTE XFER ? 

NO, BRANCH 

YES, SET FLAG FOR ODD BYTE XFER 



* SET UP FOR ISR AND ESR SCHEDULING AND EXECUTION 
* 



TLX0120 LA 


U1,TLX0130 


STH 


U1 / CCB.SUBA(UC) 


LA 


U1,TLX0240 


ST 


U1,DCB.ESR(UD) 


LH 


U1,DCB.SDN(UD) 


LA 


U0,1(UC) 


STH 


U0,ISPTAB(U1,U1) 


STH 


U0,ISPTAB(U6,U6) 


BAL 


U8 , TOCHON 


LH 


U8,DCB.ILVL(UD) 


SINT 


U8,0(U6) 


B 


EVRTE 


SPACE 




PURE 




TLX0130 EQU 


* 


L 


E5,CCB.DCB(E4) 


LH 


E7,CCB.LB0(E4) 


STH 


E7,DCB.T0UT(E5) 


LH 


E3,DCB.SDN(E5) 


OC 


E3,CLEARSEL 


WD 


E3,DCB.SADR+1(ES) 


WH 


E3,DCB.SADR+2(E5) 


WD 


E3,DCB.EADR+1(E5) 


WH 


E3,DCB.EADR+2(E5) 


EPSR 


E6,E6 


NHI 


E6,X'20FO' 


EPSR 


E7,E6 


LI 


E6,MAGHLFB 


RBT 


E6,DCB.FLG1(E5) 


BZ 


TLX0140 


OC 


E2,0DDWRITE 



GET INTERRUPT SERVICE ADDRESS 

SETUP ISR POINTER 

GET EVENT SERVICE ADDRESS 

SET ESR ADDRESS FOR SQS 

GET SELCH ADDRESS 

MAKE ODD CCB ADDRESS 

SET SELCH ISPT ENTRY 

SET CONTROLLER ISPT ENTRY 

PUT ON TIMEOUT CHAIN 

FETCH INTERRUPT LEVEL 

ENTER INTO THE ISR 

EXIT ESR STATE 



GET DCB ADDRESS 

GET CALCULATED TIME-OUT VALUE 

STORE IT 

GET SELCH ADDRESS 

CLEAR SELCH 

WRITE START ADDRESS TO SELCH 
* 

WRITE END ADDRESS TO SELCH 

* 

GET CURRENT PSW 
TURN OFF ALL INTERRUPTS 
(GO NONINTERRUPTABLE) 
CHECK THE ODD BYTE XFER FLAG 
RESET THE FLAG 
, SKIP 
GIVE CONTROLLER ODDBYTE CMD. 
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TLX0140 


EQU 


* 




oc 


E2,DCB.CENB(E5) 




oc 


E2 / DCB.CWRT(E5) 




oc 


E3,GOWRITE 




SPACE 




LX0150 


EQU 


* 




LA 


E7,TLX0190 




STH 


E7,CCB.SUBA(E4) 




LPSWR 


EO 


GO WRITE 


DC 


X ' 1400 ' 


CLEARSEL 


DC 


X ' 4800 * 


ODDWRITE 


DC 
SPACE 


X ' 4B00 * 


TLX0190 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LH 


E6,DCB.T0UT(E5) 




BZ 


TLX0195 




CLH 


E2,DCB.SDN(E5) 




BNE 


TLX0150 




LA 


E7,III 




STH 


E7,ISPTAB(E2,E2) 




LH 


E2 / DCB.DN(E5) 




SSR 


E2,E3 




THI 


E3,DU!NMTN 




BNZ 


TLX0230 




LA 


E7,TLX0210 




STH 


E7,CCB.SUBA(E4) 


TLX0195 


EQU 


* 




LPSWR 


EO 




SPACE 




TLX0210 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LH 


E6, DCB. TOUT (E5) 




BZ 


TLX0220 




CLH 


E2,DCB.DN(E5) 




BNE 


TLX0220 




THI 


E3,DU!NMTN 




BNZ 


TLX0230 


TLX0220 


EQU 


* 




LPSWR 


EO 




SPACE 




TLX0230 


EQU 


* 




STB 


E3,DCB.DDPS(E5) 



ENABLE INTERRUPTS 
START THE DRIVE 
START THE SELCH 



SET NEXT ISR ADDRESS 
* 

EXIT INTERRUPT SERVICE 
SELCH WRITE COMMAND 
CLEAR SELCH COMMAND 
ODD BYTE WRITE COMMAND 



GET DCB ADDRESS 

GET TIME-OUT CONSTANT 

IF TIMED-OUT, EXIT NOW 

FROM THE SELCH? 

NO, WAIT SOME MORE 

RESET SELCH ISPT NOW 
* 

FETCH DEVICE ADDRESS 
SENSE DEVICE STATUS 
NO MOTION OR DU?? 
YES, BRANCH 
SET NEXT ISR ADDRESS 



EXIT INTERRUPT SERVICE 



GET DCB ADDRESS 

GET TIME-OUT VALUE 

IF TIMED OUT, EXIT NOW 

FROM DEVICE? 

NO, WAIT SOME MORE 

DU OR NO MOTION? 

YES, GO PROCESS 

WAIT FOR IT TO COME AGAIN 



SAVE DRIVE STATUS 



isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
isrl 
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isr3 
isr3 
isr3 
isr3 
isr3 
isr3 
isr3 



48-190 FOO ROO 



4-17 



oc 


E2 / DCB.CDAR(E5) 


LH 


E6,DCB.T0UT(E5) 


BTFS 


2,2 


LPSWR 


EO 


LCS 


E6,l 


STH 


E6, DCB. TOUT (E5) 


L 


E6,DCB.LEAF(E5) 


ATL 


E6,SQ 


LPSWR 


EO 


SPACE 




IMPUR 




rLX0240 EQU 


* 


LHL 


UCDCB.CCB(UD) 


LHL 


U6,DCB.DN(UD) 


LH 


U7 , DCB . STAT (UD) 


THI 


U7,DU 


BP 


TLX2340 


LH 


U2 , DCB . SDN (UD) 


OC 


U2,CLEARSEL 


RDR 


U2,U0 


EXHR 


UO,UO 


RHR 


U2,U1 


OR 


UO,Ul 


C 


UO,DCB.SADR(UD) 


BM 


TLX0610 


C 


UO,DCB.EADR(UD) 


BNE 


TLX0265 


L 


UO,CCB.XLT(UC) 


ST 


UO,DCB.LLXF(UD) 


BAL 


U8 , TOCHOFF 


LH 


U7, DCB. TOUT (UD) 


BZ 


TLX0310 


LB 


U3,DCB.DDPS(UD) 


THI 


U3 , ERR ! TERR 


BNZ 


TLX0270 


TLX0250 LIS 


UO,0 


THI 


U3,X'20' 


BZ 


TLX0260 


OHI 


U0,X'9000' 


LI 


U1 / MAGWAT2B 


SBT 


U1,DCB.FLG1(UD) 


TLX0260 EQU 


* 


STH 


UO, DCB. STAT (UD) 



DISARM INTERRUPTS 
GET TIME-OUT COUNTER 
RETURN NOW IF TIMED- OUT 
DON'T RE-ADD TO S.Q. 
OTHERWISE SET MINUS TO 
SHOW WE HAVE BEEN HERE. 
GET LEAF ADDRESS 
SCHEDULE DRIVER TERMINATION 
EXIT AND WAIT FOR TERM. 



A (CCB) 

DEVICE NUMBER 

GET DEVICE DEPENDENT STATUS 

DID IT GO UNAVAILABLE 

ERROR EXIT, IF SO. 

GET THE SELCH DEVICE ADDRESS 

STOP THE SELCH 

AND OBTAIN THE SELCH FINAL 

* ADDRESS. . .PLACE IT IN 

THE APPROPRIATE POSITION. 

* 

IF THE FINAL ADDRESS LESS THAN 

THE START ADDR- SELCH ERROR. 

IS THE FINAL ADDRESS EQUAL 

TO REQUESTED END- -CHECK FURTHER. 

GET THE LENGTH OF TRANSFER 

AND SAVE IT IN THE DCB. 

REMOVE FROM TIMEOUT CHAIN 

CHECK FOR TIME OUT 

IF SO, GET OUT 

GET STATUS IN ISR 

TAPERR ? 

YES 

CLEAR STATUS 

EOT/BOT SET? 

NO - GO ON 

YES - SET USUAL STATUS 

AND SET FLAG FIELD 



STORE STATUS 



isr3 
isr3 
isr3 
isr3 
isr3 
isr3 
isr3 
isr3 
isr3 
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B 



TLX215 



GO CHECK REWIND CONDITIONS 



* CODE BELOW HERE IS EXECUTED ONLY ON ERROR CONDITIONS 



TLX0265 


EQU 


* 




S 


UO,DCB.SADR(UD) 




ST 


UO,DCB.LLXF(UD) 


TLX0270 


EQU 


* 




LB 


U0,DCB.SV1X+3(UD) 




CHI 


U0,4 • 




BE 


TLX0250 



CHECK FOR EXTENDED FUNCTION 4 
COMPUTE ACTUAL LENGTH OF TRANSFER 
AND SAVE IT IN THE DCB. 

GET USER'S OPTION CODE 

IGNORE PARITY? 

IF SO, JUST CHECK FOR EOT 



* COME HERE IF SELCH WROTE LESS THAN REQUESTED, OR IF 

* THERE WAS A TAPE ERROR AND USER DID NOT REQUEST 

* EXTENDED FUNCTION CODE 4 



LH UO,DCB.RTRY(UD) 
CH UO,DCB.RMAX(UD) 
BM TLX0300 
RETRIES EXHAUSTED-- CHECK EXTENDED OPTION CODE. 
LB UB,DCB.SV1X+3(UD) GET EXTENDED CODE 



GET RETRY COUNT 

AND COMPARE AGAINST MAX COUNT 

OK SO FAR, KEEP RETRYING 



CLH 


UB,X'8' 


BE 


TLX2390 


TLX0300 EQU 


* 


OC 


U6,DCB.CCLC(UD) 


LB 


U2,DCB.CBSR(UD) 


BAL 


UB,TLX1400 


LH 


UO,DCB.RTRY(UD) 


CH 


UO,DCB.RMAX(UD) 


BNM 


TLX2390 


AIS 


UO,l 


STH 


UO,DCB.RTRY(UD) 


BAL 


UB,TLX1760 


B 


TLX0120 


SPACE 





IS IT USER SPECIFIED NUMBER OF 
RETRIES- -DO NOT BACKSPACE 
REPORT RECOVERABLE ERROR. 

CLEAR CONTROLLER BEFORE RETRYING 

GET COMMAND BYTE 

GO TO COMMON LOGIC FOR BACKSPACE 

GET RETRY COUNT 

COMPARE TO MAX RETRIES 

FINISHED RETRIES, GET OUT 

UP RETRY COUNT 

STORE 

ERASE ONE GAP'S WORTH 

GO DO WRITE AGAIN 



esrl 

esrl 

esrl 

esrl 
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* COME HERE ONLY IF A TIME-OUT ERROR HAS OCCURRED 

* 

TLX0310 EQU * 

LHI U8,X*8282' TIMEOUT STATUS 

STH U8 , DCB . STAT (UD) STORE STATUS 



B 



TLX2150 



CHECK FOR REWIND IN PROGRESS & EXIT. 
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SPACE 

TITLE READ OPERATIONS 
********************************** 

* READ OPERATIONS 
********************************** 

TLX0320 EQU * 
* 

* ON A READ, IF WE ARE AT LOAD POINT, WE MUST ASSUME THAT 

* WE ARE GOING TO READ AT 800 BPI . UNTIL THE TAPE HAS BEEN 

* READ, ITS DENSITY IS UNKNOWN. SO, IF WE ARE AT LOAD POINT, 

* WE WILL RE-DO THE TIME-OUT CALCULATION. 
* 



TEST BOT FLAG 

IF SO, BRANCH TO RE -CALCULATE 

INITIALIZE RETRY 

COUNTER 

GET DEFAULT READ RETRY COUNT 

GET THE EXTENDED OPTIONS 

SAVE ONLY OPTION FIELD 

CHECK FOR USER RETRY COUNT 

OPTION OR 1, USE DEFAULT 

GET USER RETRY COUNT 

SET RETRY COUNT 

BEGIN READ OPERATION 

CLEAR ADDRESS SAVE AREA 

ODD BYTE XFER?(U2 =XFER SIZE) 

NO, GO PAST ODD BYTE WORK 

GET BUFFER ENDING ADDRESS 

SAVE THE END ADDRESS 

GET THE CONTENT OF NEXT BYTE 

SAVE IT 

SET UP INTERRUPT SERVICE ADDRESS 

* INTO THE CCB. 

SET THE EVENT SERVICE ROUTINE 

INTO THE DCB FOR SQS TO USE. 

GET SELCH ADDRESS 

MAKE ODD CCB ADDRESS 

SET SELCH ISPT ENTRY 

SET CONTROLLER ISPT ENTRY 

PUT ON TIMEOUT CHAIN 





LI 


U0,MAGB0TB 




TBT 


U0,DCB.FLG1(UD) 




BP 


TLX0658 


TLX0325 


EQU 


* 




LIS 


U0,0 




STH 


UO,DCB.RTRY(UD) 




LH 


UO,DCB.RRTY(UD) 




L 


Ul , DCB . SV1X (UD) 




NHI 


U1,X'1F* 




CHI 


Ul,l 




BNP 


TLX0330 




LB 


U0,DCB.SV1X(UD) 


TLX0330 


STH 


UO,DCB.RMAX(UD) 


TLX0340 


EQU 


* 




LI 


UB,0 




ST 


UB,DCB.0DDA(UD) 




THI 


U2,X'l' 




BZ 


TLX0350 




L 


Ul , DCB . EADR (UD) 




ST 


U1,DCB.0DDA(UD) 




LB 


U1,1(UB) 




STB 


Ul , DCB . ODDC (UD) 


TLX0350 


LA 


U1,TLX0360 




STH 


U1,CCB.SUBA(UC) 




LA 


Ul , TLX0470 




ST 


U1,DCB.ESR(UD) 




LH 


U1,DCB.SDN(UD) 




LA 


U0,1(UC) 




STH 


U0,ISPTAB(U1,U1) 




STH 


U0,ISPTAB(U6,U6) 




BAL 


U8,T0CH0N 
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LH 


U8,DCB.ILVL(UD) 




SINT 


U8,0(U6) 




B 


EVRTE 




SPACE 






PURE 




TLX0360 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LH 


E7,CCB.LB0(E4) 




AIS 


E7,3 




STH 


E7, DCB . TOUT (E5) 




LH 


E3,DCB.SDN(E5) 




OC 


E3,CLEARSEL 




WD 


E3,DCB.SADR+1(E5) 




WH 


E3,DCB.SADR+2(E5) 


* ADJUST 


END ADDRESS AND WRITE I 




LH 


E7,DCB.EADR+2(E5) 




OHI 


E7,l 




WD 


E3,DCB.EADR+1(E5) 




WHR 


E3,E7 




LB 


E6,DCB.CRDF(E5) 




L 


E7,DCB.SV1X(E5) 




THI 


E7,l 




BZ 


TLX0370 




LB 


E6,DCB.CRDB(E5) 


TLX0370 


EQU 


* 




STB 


E6,DCB.CMD(E5) 




EPSR 


E7,E7 




NHI 


E7,X'B7FF' 




EPSR 


E6,E7 




OC 


E2,DCB.CENB(E5) 




OC 


E2,DCB.CMD(E5) 




OC 


E 3, GORE AD 




SPACE 




TLX0380 


EQU 


* 




LA 


E7,TLX0400 




STH 


E7,CCB.SUBA(E4) 




LPSWR 


: EO 




SPACE 




GOREAD 


DC 
SPACE 


X ' 3400 ' 


TLX0400 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LH 


E6,DCB.T0UT(E5) 



FETCH INTERRUPT LEVEL 
ENTER INTO THE ISR 
RETURN FROM DRIVER 



A (DCB) 

GET CALCULATED TIME-OUT 

ADD 3 SEC FOR 25 FT. ERASED TAPE 

STORE IT 

GET SELCH ADDRESS 

CLEAR SELCH 

WRITE START ADDRESS TO SELCH 

* 

TO SELCH 

MAKE IT ODD 

WRITE END ADDRESS TO SELCH 

* 

GET FOREWARD READ COMMAND 

GET EXTENDED OPTIONS 

IS IT REALLY BACKWARD? 

NO - IS FOREWARD 

GET BACKWARD READ COMMAND 

SAVE THIS COMMAND 

GET CURRENT PSW 

TURN OFF ALL INTERRUPTS 

AND GO NON-INTERRUPTABLE 

ENABLE INTERRUPTS FROM DRIVE 

START THE DRIVE 

START THE SELCH 



SET NEXT ISR ADDRESS 
EXIT INTERRUPT SERVICE 
SELCH READ COMMAND 



GET DCB ADDRESS 
GET TIME-OUT VALUE 



dir 
dir 
dir 



isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

lsr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

isr4 

lsr4 

isr4 

isr4 

isr4 

isr4 



isr5 
isr5 
isr5 
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BZ 


TLX0410 




CLH 


E2,DCB.SDN(E5) 




BNE 


TLX0380 




LA 


£7,111 




STH 


E7,ISPTAB(E2,E2) 




SPACE 






OC 


E2,CLEARSEL 




LH 


E2,DCB.DN(E5) 




SSR 


E2,E3 




THI 


E3,DU!NMTN 




BNZ 


TLX0440 




LA 


E7,TLX0420 




STH 


E7,CCB.SUBA(E4) 


TLX0410 


EQU 


* 




LPSWR 


EO 




SPACE 




TLX0420 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LH 


E6,DCB.CCB(E5) 




BZ 


TLX0430 




CLH 


E2,DCB.DN(E5) 




BNE 


TLX0430 




THI 


E3,NMTN!EOF!DU 




BNZ 


TLX0440 


TLX0430 


EQU 


* 




LPSWR 


EO 




SPACE 




TLX0440 


EQU 


* 




STB 


E3,DCB.DDPS(E5) 




OC 


E2,DCB.DSBO(E5) 




LA 


E7,TLX0450 




STH 


E7 , CCB . SUBA (E4) 


ic 


LPSWR 


, EO 


TLX0450 


EQU 


* 




L 


E5,CCB.DCB(E4) 




RHR 


E2,E7 




STH 


E7,CCB.MISC(E4) 




OC 


E2 / DCB.CDAR(E5) 




LH 


E6,DCB.T0UT(E5) 




BNP 


TLX0460 




LCS 


E7,l 




STH 


E7,DCB.T0UT(E5) 



EXIT NOW IF TIMED OUT 

SELCH INTERRUPT? 

NOT, THE SELCH, -WAIT FOR SELCH 

SET TO IGNORE INTERRUPT 

IE THE SELCH BOTHERS US AGAIN. 

STOP SELCH 

FETCH DEVICE ADDRESS 

SENSE DEVICE STATUS 

NO MOTION OR DU? 

IF SO, PRETEND DEVICE INTEBRUPTED 

SET NEXT ISR ADDRESS 



EXIT INTERRUPT SERVICE 



GET DCB ADDRESS 

GET TIME-OUT VALUE 

IF TIMED OUT, EXIT NOW 

INT. FROM DEVICE 

NO, WAIT SOME MORE 

TERR SETS NO MOTION WITH H/W CHNG 

YES, PROCESS IT 

WAIT FOR INTERRUPT 



SAVE DRIVE STATUS 
SEND NOP CMD FOR STATUS 
SET NEXT ISR ADDRESS 
* 

EXIT INTERRUPT SERVICE 



GET CCB ADDRESS 

GET DEVICE STATUS HALFWORD 

SAVE FOR ESR USE 

NOW TURN OFF INTERRUPTS 

CHECK TIMEOUT CONSTANT 

DON'T ADD TO QUEUE TWICE. 

RESET THE TIME-OUT VALUE 



isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 
isr5 

isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 
isr6 

isr7 
lsr7 
isr7 
isr7 
isr7 
isr7 
isr7 
isr7 
isr7 
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L 


E7,DCB.LEAF(E5) 




ATL 


E7,SQ 


TLX0460 


LPSWR 

SPAC 

IMPUR 


EO 


TERMTELX 


EQU 


* 


TLX0470 


EQU 


* 




LHL 


UC,DCB.CCB(UD) 




LHL 


U6,DCB.DN(UD) 




LH 


U7 , DCB i STAT (UD) 




THI 


U7,DU 




BP 


TLX2340 




L 


U8,DCB.0DDA(UD) 




BZ 


TLX0480 




LB 


UO,DCB.ODDC(UD) 




STB 


U0,1(U8) 




LI 


UO,0 




STB 


UO,DCB.ODDC(UD) 




ST 


UO / DCB.ODDA(UD) 


TLX0480 


LHL 


U8,CCB.MISC(UC) 


* NOW READ THE 


SELCH FINAL ADDR 




LH 


U2,DCB.SDN(UD) 




OC 


U2 , CLEARSEL 




RDR 


U2,U7 




EXHR 


U7,U7 




RHR 


U2,U1 




OR 


U7,U1 




C 


U7,DCB.SADR(UD) 




BM 


TLX0610 




C 


U7 , DCB . EADR (UD) 




BNE 


TLX0522 




L 


U7,CCB.XLT(UC) 


TLX0490 


EQU 


* 




ST 


U7 , DCB . LLXF (UD) 




LH 


UO, DCB. TOUT (UD) 




BZ 


TLX0655 




BAL 


U8 , TOCHOFF 




LB 


UO,DCB.DDPS(UD) 




THI 


UO, TERR! ERR 




BNZ 


TLX0590 



GET LEAF ADDRESS 
PUT ESR ON QUEUE 
EXIT FROM ISR. 



A(CCB) 

DEVICE NUMBER 

GET DEVICE DEPENDENT STATUS 

DID IT GO OFF-LINE? 

IF SO, EXIT HERE 

GET THE CONTENT IN ADDRESS SAVE 

NOTHING, NORMAL I/O 

GET WHATEVER IN SAVE AREA 

PUT IT BACK 

REINITIALIZE SAVE AREA 



GET DEVICE STATUS HALFWORD 
! TO SEE IF WE GOT WHAT WE WANTED. 
GET THE SELCH ADDRESS 
AND ISSUE STOP & EXTENDED ADDR REA 
GET THE SELCH FINAL ADDRESS 
* 
* 

* INTO U7. 

IS FINAL ADDRESS LESS THAN START 
IF SO WE MAY HAVE TO CRASH SYSTEM. 
DID WE EXACTLY FILL OUR BUFFER? 
NO- -MAY BE SHORT READ. (CHECK MORE) 
GET THE LENGTH OF TRANSFER 

AND SAVE IT IN THE DCB. 
CHECK FOR LENGTH OF TRANSFER 

NOW REMOVE FROM TIME-OUT CHAIN 

GET DE V . DEP . STAT . 

TAPE ERROR? 

ERROR- -GO SEE WHICH ERROR 
COME HERE IF NO ERROR STATUS. FOR NORMAL I/O, THE LENGTH OF 
TRANSFER MUST BE EXACTLY AS REQUESTED, OR IT IS DEFINED TO BE 
A PARITY ERROR. 



isr7 
isr7 
isr7 



esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 
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LB 


U0,DCB.SV1X+3(UD) 




CHI 


UO,l 




BP 


TLX0530 




THI 


U8 , X * OOOl * 


* 


BZ 


TLX0530 


TLX0510 


LIS 


U0,0 


* 


ST 


UO,DCB.LLXF(UD) 


TLX0520 


EOU 


* 




LH 


U8,DCB.STAT(UD) 




THI 


U8,X'22' 




BNZ 


TLX0530 




LB 


U8,DCB.SV1X+3(UD) 




CHI 


U8,4 


* 


BE 


TLX0570 




CHI 


U8,5 




BE 


TLX0570 




LI 


U0,Y'82FA' 




STH 


UO,DCB.STAT(UD) 




B 


TLX0630 




SPACE 


** COME 


HERE 


IF WE NEED TO ADJUST 


* FINAL 

* 


ADDRESS 


TLX0522 


EQU 


* 




S 


U7,DCB.SADR(UD) 


* 


B 


TLX0490 




SPACE 


TLX0530 


EQU 


* 


* 


LIS 


U0,0 


* BUILD 

* 


A 4-BIT INDEX INTO THE STj 




LB 


U1,DCB.SV1X+3(UD) 




NHI 


Ul,l 




LR 


UO,UO 




BZ 


TLX0540 




OHI 


Ul,4 


TLX0540 


LH 


UO.DCB.STAT(UD) 



GET EXTENDED OPTION CODE 
CHECK FOR NORMAL I/O 
SPECIAL CASE - BRANCH. 
DID OVERRUN SET? 
ALL O.K. -NO ERROR- GET OUT. 

SET UP FOR EOT/EOF CHECK 
AND ZERO LENGTH OF TRANSFER 
(BY DEFINITION) 

GET THE STATUS 

END OF TAPE/END OF FILE? 

GO SET STATUS & EXIT 

IF EXTEND CODE 4, NO PARITY 

ERROR IS PERMITTED 

SO DO NORMAL EXIT, BUT 

KEEP EOF/EOT. 

BACKWARD IGNORE PARITY CODE? 

YES, BRANCH. 

DEFINE THIS AS PARITY ERROR 

* 

GO TRY AGAIN. 
LENGTH OF TRANSFER AND SELCH 



CALCULATE THE ACTUAL LENGTH OF 
AND RETURN TO MAINLINE ROUTINE 



CLEAR STATUS 



GET FOREWARD/BACKWARD FLAG 
GET PARITY ERROR FLAG 



GET EOT/BOT AND F.M. FLAGS 



esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
XFER esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
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TLX0550 

TLX0560 
TLX0570 
* IF WE 



THI 

BZ 

OHI 

THI 

BZ 

OHI 

AR 

LH 

EQU 

STH 



UO,X'02' 

TLX0550 

Ul,2 

UO,X'20' 

TLX0560 

Ul,8 

U1,U1 

U0 / TLX0580(U1) 



FILE MARK? 



EOT/BOT? 



MAKE HALE -WORD INDEX 
GET THE STATUS 



UO,DCB.STAT(UD) 



SET STATUS HERE. 
COME HERE, THE READ OPERATION WAS A SUCCESS. EXIT ESR. 
B TLX2150 CHECK FOR REWIND OP. AND EXIT. 

SPACE 



TLX0580 EQU 


* EC 


)T/1 


DC 


X'OOOO' 





DC 


X ' OOOO ' 





DC 


X'8800' 





DC 


X*8800' 





DC 


X'82FA' 





DC 


X'82EA' 





DC 


X'8AFA' 





DC 


X'8AFA' 





DC 


X'9000' 


1 


DC 


X'92FE' 


1 


DC 


X'9800* 


1 


DC 


X * 9AFE * 


1 


DC 


X*92FA' 


1 


DC 


X'92FE' 


1 


DC 


X ' 9A00 ' 


1 


DC 


X'9AFE' 


1 



,ITY 


FILE MK 


BACKWARD 





















1 







1 










1 


1 




1 










1 





1 




1 


1 





IMPOSSIBLE 


1 


1 


1 


IMPOSSIBLE 



















1 







1 










1 


1 




1 










1 





1 




1 


1 





IMPOSSIBLE 


1 


1 


1 


IMPOSSIBLE 



WE MUST HANDLE THE SITUATION WHEREBY A TAPE CANNOT BE READ 
BECAUSE OF LARGE AREAS OF 'ERASED' TAPE (CREATED BY AN 
ERASE GAP FUNCTION) . ATTEMPTS TO READ A FILE WHICH HAS AREAS 
OF ERASED TAPE RESULTS IN A DEVICE DEPENDENT STATUS OF 
X'9C (ERR , NO -MOTION, BUSY , EXAMI NE ) . THE DEVICE STATUS 
HALFWORD WILL BE A X'1000', INDICATING THAT A FILE MARK WAS 
NOT DETECTED AS EXPECTED. (EMBO - READ BY NO-OP COMMAND-X '00 ' ) 
SET A SPECIAL STATUS SO THAT THE USER MAY ISSUE A EORWARD 
RECORD COMMAND TO BYPASS THE 'ERASED' AREA OF TAPE AND PROCEED 
WITH OPERATIONS. 



esr2 
esr2 
esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 
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* MAKE SURE OTHER BITS IN EMBO ARE NOT SET- -IF THEY ARE, DO NOT 

* ASSUME THAT THE TAPE CANNOT BE READ DUE TO AREAS OF ERASED TAPE. 

* 



DON'T WIPE OUT U8 YET, WE NEED IT 
STRIP OFF LOW BITS OF HALFWORD 
FILE MARK ERROR? 
YES-GO DO SPECIAL PROCESSING 



* WE HAVE AN ERROR. WE MUST DISTINGUISH BETWEEN 'REAL' PARITY 

* ERRORS, AND SHORT READS THAT HAVE NO ERROR. WE MUST ALSO 

* TREAT NORMAL I/O AND EXTENDED OPTION I/O DIFFERENTLY. 



EQU 


* 


LR 


U0,U8 


NHI 


UO,X'FFOO' 


CHI 


UO,X'1000' 


BE 


TLX1470 



REMEMBER THAT U7 CONTAINS REQUESTED LENGTH OF TRANSFER. 
DESTROY IT, AS WE WILL USE IT LATER! 



DON'T 



IF WE HAVE AN ERROR, AND WE ARE DOING NORMAL I/O, THIS IS 
DEFINED AS A PARITY ERROR. SET THE APPROPRIATE CODE IN 
THE DCB STATUS AND RETRY. 



TLX0600 



TLX0610 



EQU 

LB 

CHI 

BNP 

LIS 

C 

BP 

B 

EQU 

OC 



U0,DCB.SV1X+3(UD) 

UO,l 

TLX0510 

UO,0 

U7,DCB.LLXF(UD) 

TLX0520 

TLX0530 

* 

U6,DCB.CCLC(UD) 



GET EXTENDED OPTION CODE 

LOOK FOR NORMAL I/O 

WE HAVE NORMAL I/O --BRANCH. 

SET UP UO FOR EOT/EOF TEST 

CHECK LENGTH OF XFER 

IF SO, IT IS AN ERROR 

CHECK EOF /EOT & QUIT. 

CLEAR CONTROLLER 



* IF WE COME HERE, THE SELCH START ADDRESS WAS GREATER THAN 

* THE SELCH FINAL ADDRESS. IF WE HAVE OVERWRITTEN O.S. CODE 

* GIVE A CRASH CODE 500. OTHERWISE, GIVE THE USER A '8484' 

* STATUS. 

HAVE WE OVERWRITTEN O.S.? 
NO- -GIVE THE USER AN ERROR. 
YES- -CRASH THE SYSTEM (SORRY!) 

SELCH ERROR ON READ OR WRITE 

STORE STATUS 

CHECK FOR RWND IN PROGRESS & EXIT 





CI 


U0,UB0T 




BP 


TLX0620 




CRSH 


502 


TLX0620 


EQU 


* 




LHI 


U8,X'8484' 




STH 


U8, DCB. STAT (UD) 




B 


TLX2150 




SPACE 




TLX0630 


EQU 


* 



esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
esr2 
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OC 


U6,DCB.CCLC(UD) 




LH 


UO / DCB.RTRY(UD) 




CH 


UO,DCB.RMAX(UD) 




BM 


TLX0640 


* RETRIES EXHAUSTED-- CHECK EXTE 




LB 


UB,DCB.SV1X+3(UD) 


£ 


CLHI 


UB,X'8' 




BE 


TLX2390 




CLHI 


UB,X'9' 




BE 


TLX2390 


TLX0640 


EQU 


* 




LB 


U2,DCB.CBSR(UD) 




LB 


UB,DCB.SV1X+3(UD) 




THI 


UB,1 




BZ 


TLX0650 




LB 


U2,DCB.CFSR(UD) 


TLX0650 


EQU 


* 




BAL 


UB,TLX1400 




LH 


UO,DCB.RTRY(UD) 




CH 


UO,DCB.RMAX(UD) 




BNM 


TLX2390 




AIS 


UO,l 




STH 


UO,DCB.RTRY(UD) 




B 


TLX0340 



CLEAR DEVICE 
GET RETRY COUNT 
AND COMPARE AGAINST MAX COUNT 
OK SO FAR, KEEP RETRYING 
D OPTION CODE. 
GET EXTENDED CODE 
IS IT USER SPECIFIED NUMBER OF 
RETRIES- -DO NOT BACKSPACE 
REPORT RECOVERABLE ERROR. 
BACKWARD OPERATION- -DO NOT 
FORWARD SPACE AFTER ERROR. 

GET COMMAND BYTE 

GET EXTENDED OPTION CODE 

IS IT ODD (IF SO BACKWARD OP) 

FORWARD OPERATION- -DO BSR. 

BACKWARD OPERATION- -DO FSR. 

GO TO COMMON LOGIC FOR BACKSPACE 

CHECK RETRY COUNTER 

COMPARE TO MAX RETRIES 

NO MORE RETRIES- -GIVE UP. 

ADD 1 TO THE COUNTER 

INCREMENT RETRY COUNT 



COME HERE ONLY IF WE TIME OUT WAITING FOR INTERRUPTS 
DURING A READ OPERATION 



TLX0655 



TLX0657 



EQU 


* 


LHI 


UO,X'2050' 


EPSR 


Ul,UO 


SSR 


U6,U2 


THI 


U2,X'91' 


BNZ 


TLX0657 


LH 


UO,DCB.MAXT(UD) 


STH 


UO,DCB.TOUT(UD) 


EPSR 


UO,Ul 


B 


EVRTE 


EQU 


* 


EPSR 


UO,Ul 


BAL 


U8 , TOCHOFF 


LHI 


U8,X'8263* 



GO NON-INTERRUPTABLE 
* 

GET DEVICE STATUS 

DID ANYTHING HAPPEN? 

YES - IT DIED OR SOMETHING 

NO - SET TIME-OUT VALUE AGAIN 

AND WAIT FOR LONG FILE (MAYBE) 

NOW GET OUT 



TIMED-OUT, REALLY - FINISH UP 
GET OFF THE TIMEOUT CHAIN 
SET UP STATUS FIELD 



esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 

esr2 
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STH U8 , DCB . STAT (UD) 
B TLX2150 



STORE STATUS esr2 

CHECK FOR RWND IN PROGRESS & EXIT esr2 



* CALCULATE THE APPROPRIATE TIME-OUT VALUE, BASED ON 

* THE ASSUMPTION THAT THE DENSITY IS 800 BPI . 



TLX0658 


EQU 


* 




LIS 


Ul,l 




LR 


U0,U2 


TLX0659 


AIS 


Ul,l 




S 


UO,DCB.XRT(UD) 




BP 


TLX0659 




STH 


U1,CCB.MISC(UC) 




B 


TLX0325 



SET UP TO CALCULATE TIME-OUT 

GET COMPUTED XFER LENGTH 

ADD 1 SECOND FOR EACH RATE SIZE 

COMPARE SIZE TO RATE AT 800 BPI 

LOOP UNTIL SIZE FIELD IS COUNTED 

SAVE TIME-OUT TEMPORARILY 

GO BACK TO NORMAL PROCESSING. 



SPACE 

TITLE COMMAND FUNCTION DECODING 
IMPUR 
TLX1280 EQU * 

* NOTE - U2 MUST BE PRESERVED IF THE REQUEST IF FOR 

* AN 'ERASE BUFFER' FUNCTION. 

CHI U3,X'C0* REWIND ? 



BACK SPACE RECORD? 



BE 


TLX1350 


CHI 


U3,X'A0' 


BE 


TLX1370 


CHI 


U3,X'90' 


BE 


TLX1360 


CHI 


U3,X'88' 


BE 


TLX1490 


CHI 


U3 / X , 84* 


BE 


TLX1600 


CHI 


U3,X'82' 


BE 


TLX1590 


CHI 


U3,X'81' 


BE 


TLX1320 


B 


TLX2360 


SPACE 




TLX1320 EQU 


* 


LA 


UB,TLX2150 


LIS 


U0,T0PT.X1B 


L 


U1,DCB.TCB(UD) 


TBT 


U0,TCB.0PT(U1) 


BZ 


TLX2360 



FOREWARD SPACE RECORD? 



WRITE FILE MARK 



FOREWARD FILE MARD 



BACKWARD FILE MARK 



DEVICE DEPENDENT FUNCTION? 



ERROR, ILLEGAL FUNCTION CODE 



SET LINK REGISTER TO CHECK RWD. 
CHECK THE EXTEND OPT IN TASK 
GET TCB ADDRESS 
CHECK THE EXTEND OPTION BIT 
EXTEND OPT IS NOT SET, BRANCH 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
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TLX1350 



LB 

CHI 

BE 

CHI 

BE 

CHI 

BE 

CHI 

BE 

B 

TITLE 

EQU 

LI 

TBT 

BNZ 

LI 

RBT 

LB 

STB 

OCR 

LHI 

SIS 

BTBS 

LI 

SBT 

B 

SPACE 

TITLE 



U1,DCB.SV1X+3(UD) 

Ul,7 

TLX1760 

Ul,10 

TLX1710 

U1,0 

TLX1700 

Ul,8 

TLX1860 

TLX2360 

REWIND 

* 

U3 , MAGBOTB 

U3,DCB.FLG1(UD) 

TLX2150 

U3 , MAGEOTB 

U3,DCB.FLG1(UD) 

U2 / DCB.CREW(UD) 

U2 , DCB . CMD (UD) 

U6,U2 

UO,200 

UO,l 

2,1 

UO,MAGREWB 

UO,DCB.FLGl(UD) 

TLX2150 



GET THE EXTENDED OPTION FIELD 
ERASE GAP? 

ERASE BUFFER? 

UNLOAD/ 

READ STATUS? 

NONE OF THE ABOVE - ILLEGAL 



IS THE TAPE AT BOT? 
* 

CHECK FOR OTHER REWINDS OCCURRING 
IS THE TAPE AT EOT? 
RESET BIT (SOON BE AT LOAD PT.) 
FETCH COMMAND 
SAVE COMMAND 
ISSUE COMMAND 
STALL FOR TIME 
(THIS IS STUPID) 



SET REWIND FLAG 

CHECK FOR OTHER REWINDS 



BACKSPACE AND FOREWARD SPACE RECORD 



* FOREWARD SPACE RECORD ENTRY POINT 



TLX1360 


EQU 


+ 




LI 


UO, MAGEOTB 




RBT 


UO,DCB.FLGl(UD) 




LB 


U2,DCB.CFSR(UD) 




B 


TLX1390 



CHECK THE EOT CONDITION 

RESET EOT FLAG 

GET COMMAND BYTE 

GO TO COMMON PROCESSING 



* BACKSPACE RECORD ENTRY POINT 
* 



TLX1370 


EQU 


* 






LI 


UO, MAGBOTB 






TBT 


UO,DCB.FLGl(UD) 


CHECK BOT FLAG 




BZ 


TLX1380 


NOT SET ! BRANCH 



dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 

dir 
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B TLX2150 
TLX1380 EQU * 

LB U2 , DCB . CBSR (UD) 



CHECK FOR REWIND CONDITIONS 
GET COMMAND BYTE. 



* COMMON BACKSPACE RECORD AND FORE WARD SPACE RECORD LOGIC 



CLEAR REGISTER 

OR STATUS 

SAVE STATUS 

CHECK FOR REWIND CONDITIONS. 

SAVE RETURN REGISTER 

SAVE COMMAND 

GET INTERRUPT SERVICE ADDRESS 

SETUP ISR POINTER 

SET THE EVENT SERVICE ADDRESS 

* INTO THE DCB FOR SQS . 

MAKE ODD CCB ADDRESS . 

SET CONTROLLER ISPT ENTRY 

GET ON TIMER CHAIN 

FETCH INTERRUPT LEVEL 

ENTER ISR 

LEVEL 

LEAF ADDRESS 

RELEASE SELCH 

RETURN FROM ESR 



A (DCB) 

ENABLE INTERRUPTS 

MAXIMUM TIMEOUT VALUE 

START TIMER 

ISSUE COMMAND 

SET NEXT ISR ADDRESS 
* 

EXIT INTERRUPT SERVICE 

GET DCB ADDRESS 

GET TIME-OUT VALUE 

IF TIMED OUT, EXIT NOW 



TLX1390 EQU 


* 


BAL 


UB,TLX1400 


LIS 


UO,0 


OH 


UO, DCB.- STAT (UD) 


STH 


UO, DCB. STAT (UD) 


B 


TLX2150 


TLX1400 EQU 


* 


ST 


UB,CCB.EBO(UC) 


STB 


U2 , DCB . CMD (UD) 


LA 


U1,TLX1410 


STH 


U1,CCB.SUBA(UC) 


LA 


U1 / TLX1460 


ST 


U1,DCB.ESR(UD) 


LA 


UO,l(UC) 


STH 


UO,ISPTAB(U6,U6) 


BAL 


U8 , TOCHON 


LH 


U8,DCB.ILVL(UD) 


SINT 


U8,0(U6) 


LI 


UE,3 


L 


UF . DCB . LEAF (UD) 


BAL 


U8,EVREL 


B 


EVRTE 


SPACE 




PURE 




TLX1410 EQU 


* 


L 


E5,CCB.DCB(E4) 


OC 


E2,DCB.CENB(E5) 


LH 


E6,DCB.MAXT(E5) 


STH 


E6, DCB. TOUT (E5) 


OC 


E2,DCB.CMD(E5) 


LA 


E7,TLX1420 


STH 


E7 / CCB.SUBA(E4) 


LPSWR 


EO 


TLX1420 EQU 


* 


L 


E5 / CCB.DCB(E4) 


LH 


E6 / DCB.CCB(E5) 


BZ 


TLX1425 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 



isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
isr8 
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THI 


E3,X'll' 




BNZ 


TLX1430 


TLX1425 


EQU 


* 




LPSWR 


EO 




SPACE 




TLX1430 


EQU 


* 




STB 


E3,DCB.DDPS(E5) 




OC 


E2,DCB.DSBO(E5) 




LA 


E7 / TLX1440 




STH 


E7 / CCB;SUBA(E4) 


* 


LPSWR 


EO 


TLX1440 


EQU 


* 




L 


E5,CCB.DCB(E4) 




RHR 


E2,E7 




STH 


E7,CCB.MISC(E4) 




OC 


E2,DCB.CDAR(E5) 




LH 


E6 / DCB.T0UT(E5) 




BNP 


TLX1450 




LCS 


E7,l 




STH 


E7 / DCB.T0UT(E5) 




L 


E7 / DCB.LEAF(E5) 




ATL 


E7,SQ 


TLX1450 


LPSWR 
SPACE 
IMPUR 


EO 


TLX1460 


EQU 


* 




LHL 


UC, DCB . CCB (UD) 




LHL 


U6 / DCB.DN(UD) 




BAL 


U8 , TOCHOFF 




LH 


U7 , DCB . TOUT (UD) 




BZ 


TLX1480 




LHL 


U8,CCB.MISC(UC) 




NHI 


US^'FFOO" 




CHI 


U8,X'1000' 




BE 


TLX1470 




LIS 


U1,0 




LH 


UB, DCB. STAT (UD) 




THI 


UB,DU!EOM!EOF 




BP 


TLX1482 




STH 


Ul, DCB. STAT (UD) 




L 


UB,CCB.EBO(UC) 




BR 


UB 



CHECK NMTN & DU 
YES, GO TOWARDS ESR 

GO WAIT FOR ANOTHER INTERRUPT 



SAVE STATUS 

SEND NOP CMD FOR STATUS 

SET NEXT ISR ADDRESS 

* 

EXIT INTERRUPT SERVICE 



GET CCB ADDRESS 

GET DEVICE STATUS HALFWORD 

SAVE FOR ESR USE 

NOW TURN OFF INTERRUPTS 

CHECK TIMEOUT CONSTANT 

DON'T ADD TO QUEUE TWICE. 

RESET THE TIME-OUT VALUE 
* 

GET LEAF ADDRESS 
PUT ESR ON QUEUE 
EXIT FROM ISR. 



A (CCB) 

DEVICE NUMBER 

REMOVE FROM TIMER CHAIN 

CHECK FOR TIME OUT 

BRANCH IF WE TIMED OUT. 

GET DEVICE STATUS HALFWORD 

MASK OFF UNWANTED BITS 

FILE MARK ERROR? 

NO, KEEP GOING 

INITIALIZE STATUS FIELD 

GET DEVICE DEPENDENT STATUS 

DID SOMETHING UNUSUAL HAPPEN? 

IF SO GO TO SPECIAL LOGIC 

SETS ZERO STATUS 

RESTORE LINK REGISTER 

EXIT 



isr8 
isr8 
isr8 
isr8 

isr9 
isr9 
±sr9 
isr9 
isr9 
isr9 

isra 
isra 
isra 
isra 
isra 
isra 
isra 
isra 
isra 
isra 
isra 
isra 



esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
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TLX1470 EQU * 

* SET SPECIAL STATUS FOR FILE MARK ERROR ON ERASED TAPE. 



FILE MARK ERROR STATUS 

GET THE DEVICE DEPENDENT STATUS 

WAS THERE ALSO END OF TAPE? 

IF EOT, GO CHECK FOR BOT/EOT 

SAVE THE STATUS 

AND GO CHECK REWIND STATUS 



DISARM INTERPT 

TIMEOUT ON BACKSPACE RECORD 

STORE STATUS 

CHECK FOR RWND IN PROGRESS & EXIT 



* COME HERE ON FSR OR BSR OPERATION ONLY IF DU,EOM,OR EOF IS 

* SET AT THE CONCLUSION OF THE OPERATION. 



LHI 


U1,X'82AA* 


LH 


UB, DCB. STAT (UD) 


THI 


UB,EOM 


BNZ 


TLX1485 


STH 


Ul , DCB . STAT (UD) 


B 


TLX2150 


* TIMEOUT ESR 


FOR BACKSPACE AN 


TLX1480 EQU 


* 


OC 


U6 , DCB . CDAR (UD) 


LHI 


U8,X'8271' 


STH 


U8, DCB. STAT (UD) 


B 


TLX2150 



TLX1482 


EQU 


* 




THI 


UB,DU 




BP 


TLX2340 




THI 


UB,EOF 




BZ 


TLX1485 




OHI 


ui,x'8800' 




STH 


Ul , DCB . STAT (UD) 


TLX1485 


EQU 


* 




BAL 


U9 / TLX2050 




LI 


U8,MAGE0TB 




TBT 


U8,DCB.FLG1(UD) 




BZ 


TLX1487 




OHI 


Ul , X ' 9000 * 


TLX1487 


EQU 


* 




STH 


Ul , DCB . STAT (UD) 




B 


TLX2150 




TITLE 


WRITE FILE MARK 


TLX1490 


EQU 


* 


* 


BAL 


UB,TLX1940 


* SET UP 

* 


RETRY 


COUNTERS 




LIS 


U0,0 




STH 


UO,DCB.RTRY(UD) 



DID DRIVE GO OFF-LINE? 

IF SO, GET OUT. 

WAS IT END-OF-FILE? 

IF NOT SKIP TO END/BEGIN OF TAPE 

SET END OF FILE STATUS. 

SAVE THE STATUS 

BRANCH HERE IF EOM IS SET 

GO SEE IF WE ARE AT EOT OR BOT 

NOW TEST FOR EOT. 

NO EOT, GO CHECK REWIND STATUS 
YES, IS EOT, SET STATUS. 



AND THEN CHECK REWIND STATUS 



CHECK WRITE PROTECTED - 

WILL NOT RETURN IF DRIVE! PROTECTED 



INITIALIZE RETRY 
COUNTER 



esr3 
esr3 
esr3 
esr3 

esr3 
esr3 
esr3 

esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 
esr3 

dir 
dlr 
dir 
dir 
dir 
dir 
dir 
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LH 


Ul , DCB . WRY1 (UD) 




L 


U0,DCB.SV1X(UD) 




BZ 


TLX1500 




LB 


U1,DCB.SV1X(UD) 


TLX1500 

* 


STH 


U1,DCB.RMAX(UD) 


* SET UP 

* 


FOR ESR AND ISR SCHEDU 


TLX1510 


EQU 


* 




LB 


U2 , DCB . CWFM (UD) 




STB 


U2 , DCB . CMD (UD) 




LA 


U1,TLX1520 




STH 


U1 / CCB.SUBA(UC) 




LA 


U1,TLX1550 




ST 


U1,DCB.ESR(UD) 




LA 


UO / l(UC) 




STH 


UO,ISPTAB(U6,U6) 




BAL 


U8 , TOCHON 




LH 


U8,DCB.ILVL(UD) 




SINT 


U8,0(U6) 




LI 


UE,3 




L 


UF, DCB. LEAF (UD) 




BAL 


U8,EVREL 




B 


EVRTE 




SPACE 






PURE 




TLX1520 


EQU 


* 




L 


E5,CCB.DCB(E4) 




OC 


E2,DCB.CENB(E5) 




LH 


E6 / DCB.MAXT(E5) 




STH 


E6,DCB.T0UT(E5) 




OC 


E2,DCB.CMD(E5) 




LA 


E7,TLX1530 




STH 


E7,CCB.SUBA(E4) 




LPSWR 


EO 


TLX1530 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LH 


E6,DCB.CCB(E5) 




BZ 


TLX1535 




STB 


E3,DCB.DDPS(E5) 




THI 


E3,X , 11' 




BNZ 


TLX1540 


TLX1535 


EQU 


* 



GET DEFAULT WRITE RETRY COUNT 
GET EXTENDED FUNCTION CODE 
IF EXT. FNCTN = O, USE DEFAULT 
IF NOT, USE USER'S COUNT 
SET RETRY COUNT. 



FETCH COMMAND 

SAVE COMMAND 

SET THE INTERRUPT SERVICE ADDR 

*INTO THE ISPT. 

SET THE EVENT SERVICE ADDRESS 

* INTO THE DCB FOR SQS . 

MAKE ODD CCB ADDRESS 

SET CONTROLLER ISPT ENTRY 

PUT ONTO TIMER CHAIN 

FETCH INTERRUPT LEVEL 

ENTER ISR 

LEVEL 

LEAF ADDRESS 

RELEASE SELCH 

RETURN FROM ESR 



A (DCB) 

ENABLE INTERRUPTS 

MAXIMUM TIMEOUT VALUE 

START TIMER 

ISSUE COMMAND 

GET NEXT ISR ADDRESS 

* 

EXIT INTERRUPT SERVICE 

GET DCB ADDRESS 

GET TIME-OUT VALUE 

IF TIMED OUT, EXIT NOW 

SAVE STATUS 

CHECK NMTN & DU 

YES, GO TOWARDS ESR 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 



isrb 
isrb 
isrb 
isrb 
isrb 
isrb 
isrb 
isrb 
isrb 
isrc 
isrc 
isrc 
isrc 
isrc 
isrc 
isrc 
isrc 
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LPSWR EO 

SPACE 
TLX1540 EQU * 

OC E2,DCB.CDAR(E5) 

LH E6,DCB.TOUT(E5) 

BTFS 2 , 2 

LPSWR EO 

LCS E6,l 

STH E6,DCB.T0UT(E5) 

L E6, DCB. LEAF (E5) 

ATL E6,SQ 

LPSWR EO 

SPACE 

IMPUR 
TLX1550 EQU * 

LHL 

LHL 

BAL 

LH 

BZ 

LH 

THI 

BP 

THI 

BZ 

LIS 

THI 

BZ 

OHI 

LI 

SBT 
TLX1560 EQU 

STH 

B 
TLX1570 EQU 



UC, DCB . CCB (UD) 

U6,DCB.DN(UD) 

U8,TOCHOFF 

U8, DCB. TOUT (UD) 

TLX1570 

UB, DCB. STAT (UD) 

UB,DU 

TLX2340 

UB,X'0002' 

TLX1580 

UO,0 

UB,X'20' 

TLX1560 

UO,X'9000' 

U1,MAGWAT2B 

U1,DCB.FLG1(UD) 
* 

UO, DCB. STAT (UD) 
TLX2150 

* 



GO WAIT FOR ANOTHER INTERRUPT 



TURN OFF INTERRUPTS 
GET TIME-OUT COUNTER 
RETURN NOW IF TIMED-OUT 
DON'T RE-ADD TO S.Q. 
OTHERWISE SET MINUS TO 
SHOW WE HAVE BEEN HERE. 
GET LEAF ADDRESS 
SCHEDULE DRIVER TERMINATION 
EXIT AND WAIT FOR TERM. 



A (CCB) 

DEVICE NUMBER 

REMOVE FROM TIMER CHAIN 

CHECK FOR TIME-OUT 

TIMED OUT? YES, BRANCH 

GET DEVICE DEPENDENT STATUS 

DID WE GO DU? 

IF SO, EXIT. 

IS TAPE MARK STATUS SET? 

NO, GO RETRY 

EOT/BOT SET? 

NO - GO ON 

YES - SET USUAL STATUS 

AND SET FLAG FIELD 



* TIME OUT ON WRITE FILE MARK 
SSR U6,U1 



PLACE FOR THE USER 

EXIT AND CHECK FOR REWINDS 

OPERATI ON . 

SENSE STATUS 



THI 

BNZ 

LHI 

STH 

B 

SPACE 



U1,DU 

TLX2340 

U8,X'8275' 

U8, DCB. STAT (UD) 

TLX2150 



INDICATE TIME OUT ON WFM. 

STORE STATUS 

CHECK FOR RWND IN PROGRESS & EXIT 



isrc 

isrd 
isrd 
isrd 
isrd 
isrd 
isrd 
isrd 
isrd 
isrd 
isrd 



esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
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TLX1580 EQU 


* 


LB 


U2,DCB.CBSR(UD) 


BAL 


UB,TLX1400 


LH 


UO / DCB.RTRY(UD) 


CH 


UO,DCB.RMAX(UD) 


BNM 


TLX2370 


AIS 


U0,1 


STH 


UO,DCB.RTRY(UD) 


B 


TLX1510 


SPACE 




TITLE 


FORWARD FILE MARK 



GET COMMAND BYTE 

GO TO COMMON LOGIC FOR BACKSPACE 

RETRY COUNTS 

COMPARE TO MAX 

UP RETRY COUNT 

STORE IT 

ATTEMPT TO WRITE FM 

AND BACK FILE MARK 



esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 
esr4 



* BACK FILE MARK ENTRY 
* 



TLX1590 



EQU 

LI 

TBT 

LB 

BZ 

B 

SPACE 



UO , MAGBOTB 
UO,DCB.FLGl (UD) 
U2,DCB.CBFM(UD) 
TLX1610 
TLX2150 



CHECK BOT FLAG 

GET COMMAND BYTE 

NOT SET ! BRANCH 

GO CHECK REWIND CONDITIONS 



* FORE WARD FILE MARK ENTRY 
* 



TLX1600 



EQU 

LI 

RBT 

LB 

SPACE 



UO,MAGEOTB 

UO,DCB.FLGl(UD) 

U2,DCB.CFFM(UD) 



CHECK THE EOT CONDITION 
RESET EOT FLAG 
FETCH COMMAND 



* COMMON BACKFILE AND FOREWARD FILE LOGIC STARTS HERE 
* 



TLX1610 EQU 


* 




STB 


U2, 


DCB . CMD (UD) 


LA 


Ul, 


TLX1620 


STH 


Ul, 


.CCB.SUBA(UC) 


LA 


Ul, 


, TLX1650 


ST 


Ul. 


.DCB.ESR(UD) 


LA 


UO, 


, 1 (UC) 


STH 


uo, 


, isptab(U6,u6) 


BAL 


U8, 


. TOCHON 


LH 


U8. 


,DCB.ILVL(UD) 


SINT 


U8. 


, 0(U6) 



SAVE COMMAND 

SET THE INTERRUPT SERVICE ADDR 

* INTO THE CCB. 

SET THE EVENT SERVICE ADDRESS 

* INTO THE DCB FOR SQS . 
MAKE ODD CCB ADDRESS 

SET CONTROLLER ISPT ENTRY 
PUT ONTO TIMER CHAIN 
FETCH INTERRUPT LEVEL 
ENTER ISR 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
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LI 


UE,3 


LEVEL 


dir 




L 


UF,DCB.LEAF(UD) 


LEAF ADDRESS 


dir 




BAL 


U8,EVREL 


RELEASE SELCH 


dir 




B 


EVRTE 


RETURN FROM ESR 


dir 




SPACE 










PURE 






isre 


TLX1620 


EQU 


* 




isre 




L 


E5,CCB.DCB(E4) 


A (DCB) 


isre 




OC 


E2,DCB.CENB(E5) 


ENABLE INTERRUPTS 


isre 




LH 


E6,DCB.MAXT(E5) 


MAXIMUM TIMEOUT VALUE 


isre 




STH 


E6,DCB.T0UT(E5) 


START TIMER 


isre 




OC 


E2,DCB.CMD(E5) 


ISSUE COMMAND 


isre 




LA 


E7,TLX1630 


SET NEXT ISR ADDRESS 


isre 




STH 


E7,CCB.SUBA(E4) 


* 


isre 




LPSWR 


EO 


EXIT INTERRUPT SERVICE 


isre 


TLX1630 


EQU 


* 




isre 




L 


E5,CCB.DCB(E4) 


GET DCB ADDRESS 


isre 




LH 


E6,DCB.CCB(E5) 


GET TIME-OUT VALUE 


isre 




BZ 


TLX1635 


IF TIMED OUT, EXIT NOW 


isre 




THI 


E3,X'll' 




isre 




BNZ 


TLX1640 


YES, GO TOWARDS ESR 


isre 


TLX1635 


EQU 


* 




isre 




LPSWR 


EO 


GO WAIT FOR ANOTHER INTERRUPT 


isre 




SPACE 








TLX1640 


EQU 


* 




isrf 




STB 


E3,DCB.DDPS(E5) 


SAVE STATUS 


isrf 




OC 


E2,DCB.CDAR(E5) 


TURN OFF INTERRUPTS 


isrf 




LH 


E6,DCB.T0UT(E5) 


GET TIME-OUT COUNTER 


isrf 




BTFS 


2,2 


RETURN NOW IF TIMED-OUT 


isrf 




LPSWR 


EO 


DON'T RE-ADD TO S.Q. 


isrf 




LCS 


E6.1 


OTHERWISE SET MINUS TO 


isrf 




STH 


E6, DCB. TOUT (E5) 


SHOW WE HAVE BEEN HERE. 


isrf 




L 


E6, DCB. LEAF (E5) 


GET LEAF ADDRESS 


isrf 




ATL 


E6,SQ 


SCHEDULE DRIVER TERMINATION 


isrf 




LPSWR 


EO 


EXIT AND WAIT FOR TERM. 


isrf 




SPACE 










IMPUR 






esr5 


TLX1650 


EQU 


* 




esr5 




LHL 


UCDCB.CCB(UD) 


A (CCB) 


esr5 




LHL 


U6,DCB.DN(UD) 


DEVICE NUMBER 


esr5 




LH 


U7,DCB.T0UT(UD) 


CHECK FOR TIME OUT 


esr5 




BZ 


TLX1680 


TIMED OUT? YES, BRANCH 


esrS 




BAL 


U8,T0CH0FF 


REMOVE FROM TIMEOUT CHAIN 


esr5 
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LH 


UB,DCB.STAT(UD) 




THI 


UB,DU 




BP 


TLX2 340 




LIS 


UO,0 




THI 


UB,X'0002' 




BZ 


TLX1670 




THI 


UB,EOM 




BNZ 


TLX1660 




STH 


UO,DCB.STAT(UD) 




B 


TLX2150 


TLX1660 


EQU 


* 




LI 


U1,MAGWAT2B 




SBT 


U1,DCB.FLG1(UD) 




LHI 


UO,X'9000' 




STH 


UO / DCB.STAT(UD) 




B 


TLX2150 


TLX1670 


EQU 


* 


* NO EOF 


DETECTED- -THIS IS O.K 


* WHEN THE TAPE IS AT LOAD POI; 




LB 


U1,DCB.FC(UD) 




CHI 


U1,X'82' 




BNE 


TLX2350 




THI 


UB,EOM 




BZ 


TLX2350 




STH 


UO,DCB.STAT(UD) 




B 


TLX2150 



TLX1680 



SPACE 

EQU 

LHI 

EPSR 

SSR 

THI 

BNZ 

LH 

STH 

EPSR 

B 



TLX1690 



U0,X'2050' 

Ul,UO 

U6,U2 

U2,X'D1' 

TLX1690 

UO,DCB.MAXT(UD) 

UO,DCB.TOUT(UD) 

UO,Ul 

EVRTE 

* 



GET THE STATUS FIELDS 

DID WE GO OFF-LINE? 

GET OUT, IF SO 

CLEAR STATUS HERE. 

WE MUST BE ON A FILEMARK. 

CHECK TYPE OF OPERATION 

END OF TAPE CONDITION? 

END OF TAPE DETECTED 

SET STATUS FINALLY. 

GO CHECK FOR REWIND CONDITIONS. 

SET EOT FLAG 

* 

INDICATE EOT IN STATUS FIELD 

SET STATUS FINALLY. 

GO CHECK FOR REWIND CONDITIONS. 

ONLY ON BACKFILE OPERATIONS 

r 

GET THE FUNCTION 

BACK FILE OPERATION? 

UNRECOVERABLE ERROR -NO FILEMARK 

END OF TAPE CONDITION? 

NO - REALLY AN ERROR. 

SAVE THE STATUS 

GO CHECK REWIND CONDITIONS. 



GO NON-INTERRUPTABLE 

* 

GET DEVICE STATUS 

DID ANYTHING HAPPEN? 

YES - IT DIED OR SOMETHING 

NO - SET TIME-OUT VALUE AGAIN 

AND WAIT FOR LONG FILE (MAYBE) 

NOW GET OUT 

* 



TIMED-OUT, REALLY - FINISH UP 



EQU 

EPSR UO,Ul 

* TIMEOUT ON FILE MARK OPERATION. 

* REMOVE FROM TIMEOUT CHAIN NOW. HOWEVER, WHEN PERFORMING LONG 

* FORWARD AND BACK FILE OPERATIONS, WE MAY TIMEOUT SEVERAL TIMES 

* WITHOUT EVER REPORTING THE TIMEOUT TO THE USER. THEREFORE 



esr5 

esr5 
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* WE MUST STAY ON THE TIMEOUT CHAIN UNTIL WE ARE READY TO GIVE 

* UP AND GIVE THE USER A TIMEOUT STATUS. 

REMOVE FROM TIMER CHAIN. 
SET TIME OUT FOR ERROR MESSAGE 
STORE STATUS 
CHECK FOR RWD IN PROGRESS & EXIT 

DEVICE DEPENDENT FUNCTION CODE O 

FETCH COMMAND 

SAVE COMMAND 

ISSUE COMMAND 

STALL FOR TIME TO BE SURE 

THE COMMAND DOES NOT GET 

CLEARED BY THE NEXT OPERATION. 

SET REWIND/UNLOAG FLAG 

BRANCH TO CHECK REWIND COMPLETE 

TITLE ERASE - DEVICE DEPENDENT FUNCTION CODES 7 AND 10 
* 

* SET UP TO PERFORM THE SOFTWARE 'ERASE BUFFER* OPERATION. 

* THIS WILL REPEATEDLY CALL A ROUTINE (TLX1760) TO PERFORM 

* THE HARDWARE ERASE GAP OPERATION. 

* 

* ENTER WITH U2 CONTAINING AN INDEX THAT WILL GIVE THE 

* PROPER 'BYTES PER GAP' 





BAL 


U8 , TOCHOFF 




LHI 


U8 / X'8272' 




STH 


U8,DCB.STAT(UD) 




B 


TLX2150 




TITLE 


REWIND & UNLOAD 


TLX1700 


EQU 


* 




LB 


U2 / DCB.CUNL(UD) 




STB 


U2,DCB.CMD(UD) 




OCR 


U6,U2 




LHI 


U0,250 


TLX1705 


SIS 


U0,1 




BP 


TLX1705 




LI 


UO,MAGUNLB 




SBT 


U0,DCB.FLG1(UD) 




B 


TLX2150 



TLX1710 



TLX1740 



TLX1750 



EQU 

LIS 

D 

LR 

BZ 

AIS 

EQU 

STH 

SPACE 

EQU 

BAL 

LCS 

AHM 

BP 

B 



U8,0 

U8,DCB.BPG(UD,U2) 

U8,U8 

TLX1740 

U9,l 

* 

U9,DCB.ESCT(UD) 



UB,TLX1760 

U0,1 

UO,DCB.ESCT(UD) 

TLX1750 

TLX2150 



SET UP REG TO COUNT GAPS TO ERASE 
COMPUTE GAPS NEEDED FOR ERASE 

NO REMAINDER- -BRANCH 
ADJUST UPWARD 

SAVE COUNT 



ERASE ONE GAP'S WORTH 

DECREMENT COUNT 
MORE, LOOP 
ALL DONE. 
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* FOLLOWING ROUTINE EXECUTES ONE 

* 


TLX1760 EQU 


* 


ST 


UB,CCB.EBO(UC) 


LI 


U1,MAGWAT2B 


TBT 


U1,DCB.FLG1(UD) 


BZ 


TLX1770 


LHI 


U0,X'9000' 


STH 


UO, DCB. STAT (UD) 


B 


TLX2150 


TLX1770 EQU 


* 


BAL 


UB,TLX1940 


LB 


U2,DCB.CERS(UD) 


STB 


U2,DCB.CMD(UD) 


LA 


U1.TLX1780 


STH 


Ul . CCB . SUBA (UC) 


LA 


U1,TLX1810 


ST 


U1,DCB.ESR(UD) 


LA 


U0,1(UC) 


STH 


UO, ISPTAB(U6,U6) 


BAL 


U8 , TOCHON 


LH 


U8 / DCB.ILVL(UD) 


SI NT 


U8,0(U6) 


LI 


UE,3 


L 


UF , DCB . LEAF (UD) 


BAL 


U8,EVREL 


B 


EVRTE 


SPACE 




PURE 




TLX1780 EQU 


* 


L 


E5,CCB.DCB(E4) 


OC 


E2,DCB.CENB(E5) 


LH 


E6,DCB.MAXT(E5) 


STH 


E6, DCB. TOUT (E5) 


OC 


E2,DCB.CMD(E5) 


LA 


E7,TLX1790 


STH 


E7, CCB. SUBA (E4) 


LPSWR 


EO 


TLX1790 EQU 


* 


L 


E5,CCB.DCB(E4) 


LH 


E6,DCB.CCB(E5) 


BZ 


TLX1795 


THI 


E3,X'13' 



ERASE GAP OPERATION 



SAVE LINK REGISTER 

CHECK TO SEE IF EOT CAME UP 

* 

NO, JUMP TO CONTINUE OPERATION 
AT EOT GIVE USER X" 9000 ' STATUS 
* 



GO CHECK FOR WRITE -RING 

FETCH COMMAND 

SAVE COMMAND 

SET THE INTERRUPT SERVICE ADDR 

* INTO THE CCB. 

SET THE EVENT SERVICE ADDRESS 

*INTO THE DCB FOR SQS . 

MAKE ODD CCB ADDRESS 

SET CONTROLLER ISPT ENTRY 

PUT ONTO TIMER CHAIN 

FETCH INTERRUPT LEVEL 

ENTER ISR 

LEVEL 

LEAF ADDRESS 

RELEASE SELCH 

RETURN FROM ESR 



A (DCB) 

ENABLE INTERRUPTS 

MAXIMUM TIMEOUT VALUE 

START TIMER 

ISSUE COMMAND 

SET NEXT ISR ADDRESS 
* 

EXIT INTERRUPT SERVICE 

GET DCB ADDRESS 

GET TIME-OUT VALUE 

IF TIMED OUT, EXIT NOW 

CHECK EOM OR NO MOTION FOR 6250 



dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 
dir 

isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 
isrg 



48-190 FOO ROO 



4-39 





BNZ 


TLX1800 


TLX1795 


EQU 


* 




LPSWR 


EO 




SPACE 




TLX1800 


EQU 


* 




STB 


E3,DCB.DDPS(E5) 




OC 


E2, DCB. CDAR (E5) 




LH 


E6, DCB. TOUT (E5) 




BTFS 


2,2 




LPSWR 


EO 




LCS 


E6,l 




STH 


E6 , DCB. TOUT (E5) 




L 


E6, DCB. LEAF (E5) 




ATL 


E6,SQ 




LPSWR 


EO 




SPACE 






IMPUR 




TLX1810 


EQU 


* 




LHL 


UCDCB.CCB(UD) 




LHL 


U6,DCB.DN(UD) 




BAL 


U8 , TOCHOFF 




LH 


U7, DCB. TOUT (UD) 




BZ 


TLX1820 




LH 


UB, DCB. STAT (UD) 




THI 


UB,DU 




BP 


TLX2340 




LIS 


UO,0 




THI 


UB,EOM 




BP 


TLX1840 




STH 


UO, DCB. STAT (UD) 




L 


UB,CCB.EBO(UC) 




CR 


UB,UB 




BR 


UB 


TLX1820 


EQU 


* 


*TIME OUT ON ERASE 




OC U6 , DCB . CDAR (UD) 




LHI 


U8,X'8273' 




STH 


U8, DCB. STAT (UD) 




B TLX2150 



TLX1840 EQU * 
*SET EOM ON ERASE 

LI Ul , MAGWAT2B 



YES, GO TOWARDS ESR 



GO WAIT FOR ANOTHER INTERRUPT 



SAVE STATUS 

TURN OFF INTERRUPTS 

GET TIME-OUT COUNTER 

RETURN NOW IF TIMED-OUT 

DON'T RE-ADD TO S.Q. 

OTHERWISE SET MINUS TO 

SHOW WE HAVE BEEN HERE. 

GET LEAF ADDRESS 

SCHEDULE DRIVER TERMINATION 

EXIT AND WAIT FOR TERM. 



A(CCB) 

DEVICE NUMBER 

GET OFF TIMEOUT CHAIN 

CHECK FOR TIME-OUT 

BRANCH IF WE TIMED OUT 

GET DEVICE DEPENDENT STATUS 

DID IT GO OFF LINE? 

IF SO, EXIT NOW 

CLEAR REGISTER 

CHECK FOR END OF TAPE 

EOT SET- -BRANCH 

PLACE FOR THE USER 

GET LINK REGISTER 

MUST SET CC=0 

AND RETURN TO CALLER. 



DISARM INTRPT 

TIMEOUT STATUS 

STORE STATUS 

CHECK FOR RWND IN PROGRESS & EXIT 



SET EOT FLAG IN DCB 
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SBT 

LHI 

STH 

B 

SPACE 



U1,DCB.FLG1(UD) 
U8,X'9000' 
U8,DCB.STAT(UD) 
TLX2150 



SET STATUS TO X v 9000' 

STORE STATUS 

CHECK FOR RWND IN PROGRESS & EXIT 



esr6 
esr6 
esr6 
esr6 



TITLE 


READ STATUS - DEVICE 


TLX1860 EQU 


* 


L 


U1,CCB.XLT(UC) 


CLI 


Ul,8 • 


BL 


TLX2360 


LIS 


U8,3 


STH 


U8, DCB. TOUT (UD) 


LA 


U8,TLX1920 


ST 


U8,DCB.ESR(UD) 


LA 


U8,TLX1870 


STH 


U8 , CCB . SUBA (UC) 


LA 


U8,1(UC) 


STH 


U8,ISPTAB(U6,U6) 


BAL 


U8 , TOCHON 


OC 


U6,DCB.CENB(UD) 


OC 


U6,DCB.DSB0(UD) 


B 


EVRTE 


PURE 




TLX1870 THI 


E3,X*10' 


BNP 


TLX1910 


L 


E5 / CCB.DCB(E4) 


RH 


E2,DCB.STAO(E5) 


LA 


E7,TLX1880 


STH 


E7, CCB. SUBA (E4) 


OC 


E2,DCB.DSB1(E5) 


LPSWR 


EO 


TLX1880 THI 


E3,X'10' 


BNP 


TLX1910 


L 


E5,CCB.DCB(E4) 


RH 


E2,DCB.STA1(E5) 


LA 


E7,TLX1890 


STH 


E7,CCB.SUBA(E4) 


OC 


E2,DCB.DSB2 (E5) 


LPSWR 


EO 


TLX1890 THI 


E3,X'10' 


BNP 


TLX1910 


L 


E5,CCB.DCB(E4) 



DEPENDENT FUNCTION CODE 8 

GET REQUESTED LENGTH OF XFER 

BUFFER SIZE LESS THAN 8 ? 

BUFFER IS TOO SMALL 

SET A SHORT TIME-OUT CONSTANT 

* 

GET ADDRESS OF OUR ESR 

NOW HAVE ESR ADDR SET UP 

GET ADDRESS OF FIRST ISR 

PUT IN CCB FOR INT SERV 

GET CCB ADDR + 1 

ISPT NOW SET UP 

GET ON TIME-OUT CHAIN 

ENABLE INTERRUPTS 

ASK FOR FIRST HALFWORD 



DO WE HAVE NO-MOTION 

NO - WAIT SOME MORE 

GET DCB ADDRESS 

GET THE HALFWORD 

GET NEXT ISR ADDRESS 

SET UP CCB 

ASK FOR NEXT HALF WORD 

DO WE HAVE NO-MOTION 

NO - WAIT SOME MORE 

GET DCB ADDRESS 

GET THE HALFWORD 

GET NEXT ISR ADDRESS 

SET UP CCB 

ASK FOR NEXT HALF WORD 

DO WE HAVE NO-MOTION 
NO - WAIT SOME MORE 
GET DCB ADDRESS 
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RH 


E2,DCB.STA2(E5) 




LA 


E7,TLX1900 




STH 


E7,CCB.SUBA(E4) 




OC 


£2,008.0363 (E5) 




LPSWR 


EO 


TLX1900 


THI 


E3,X'10' 




BNP 


TLX1910 




L 


E5,CCB.DCB(E4) 




RH 


E2,DCB.STA3(E5) 




LH 


E7,DCB.T0UT(E5) 




BNP 


TLX1910 




LCS 


E7,l 




STH 


E7, DCB. TOUT (E5) 




LA 


E7,III 




STH 


E7,ISPTAB(E2,E2) 




L 


E7 / DCB.LEAF(E5) 




ATL 


E7,SQ 


TLX1910 


LPSWR 
IMPUR 


EO 


TLX1920 


EQU 


* 




LHL 


U6,DCB.DN(UD) 




LHL 


UC,DCB.CCB(UD) 




BAL 


U8 , TOCHOFF 




LH 


Ul, DCB. TOUT (UD) 




BZ 


TLX1930 




L 


U1,DCB.SADR(UD) 




LH 


UO,DCB.STAO(UD) 




STH 


U0,0(U1) 




LH 


U0,DCB.STA1(UD) 




STH 


U0,2(U1) 




LH 


U0,DCB.STA2(UD) 




STH 


U0,4(U1) 




LH 


U0,DCB.STA3(UD) 




STH 


U0,6(U1) 




B 


TLX2150 


TLX1930 


EQU 


* 




LHI 


U8,X'82DD' 




STH 


U8 , DCB . STAT (UD) 




B 


TLX2150 




TITLE 


SUPPORT SUBROUTINES 


* * * * 


* * * 


*********** 



GET THE HALFWORD 

GET NEXT ISR ADDRESS 

SET UP CCB 

ASK FOR NEXT HALF WORD 

DO WE HAVE NO-MOTION 

NO - WAIT SOME MORE 

GET DCB ADDRESS 

GET THE HALFWORD 

DID WE TIME OUT? 

NO - NOTHING ELSE TO DO 

RESET THE TIME-OUT CONSTANT 

SO WE DO NOT CRASH SOMETIMES 

RESET THE ISPT 
* 

SCHEDULE ESR 
* 



WILL RE-ENTER HERE 
RE -SET SOME POINTERS 

* 

GET OFF TIME-OUT CHAIN 

DID WE TIME OUT? 

YES - BRANCH TO HANDLE TIMEOUT 

GET USER BUFFER ADDRESS 

MOVE DATA TO USER BUFFER 



COME HERE ONLY ON TIME-OUT 

SET A TIME-OUT FLAG 

STORE STATUS 

CHECK FOR RWND IN PROGRESS & EXIT 
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SUPPORT SUBROUTINES 



4-42 



48-190 FOO ROO 



IMPUR 



BAL UB,TLX1940 



* THIS ROUTINE IS CALLED FROM OPERATIONS WHICH PERFORM WRITE 

* FUNCTIONS (WRITE, WRITE GAPLESS, WRITE FILEMARK, AND ERASE) 

* TO SEE IF THE DRIVE IS WRITE PROTECTED. IF THE DRIVE IS 

* WRITE PROTECTED, THIS ROUTINE SETS AN '8283' STATUS AND EXITS. 

* IF THE DRIVE MAY BE PLACED IN A WRITE MODE, THIS ROUTINE 

* RETURNS TO THE CALLER. 



TLX1940 EQU 


* 


ST 


UB,CCB.EB1(UC) 


LA 


U8,TLX1990 


ST 


U8,DCB.ESR(UD) 


LA 


U8,TLX1950 


STH 


U8,CCB.SUBA(UC) 


LA 


U8,1(UC) 


STH 


U8,ISPTAB(U6,U6) 


LIS 


U8,3 


STH 


U8 , DCB . TOUT (UD) 


BAL 


U8 , TOCHON 


OC 


U6,DCB.CENB(UD) 


OC 


U6,DCB.DSBO+l(UD) 


B 


EVRTE 



SAVE RETURN ADDR IN SCRATCH AREA 

ADDRESS OF ESR FOR RING 

SET NEW ESR ENTRY 

SET UP FIRST RING ISR 

* 

MAKE ADDRESS ODD FOR CCB 

* AND SET IN ISPT 

SET A SHORT TIME-OUT VALUE 

* 

GET ON TIME-OUT CHAIN 
ENABLE INTERRUPTS AND 
ISSUE SENSE COMMAND (X'30') 
EXIT FROM ESR 



* INTERRUPT SERVICE 



PURE 
TLX1950 EQU * 

LA E7,TLX1960 
STH E7,CCB.SUBA(E4) 
RH E2,CCB.MISC(E4) 
LPSWR EO 



NEXT RING ISR 

* MUST BE SAVED IN CCB 

READ THE HALFWORD WE NEED 

WAIT FOR BUSY TO DROP TO GIVE 

US THE NEXT INTERRUPT. 



TLX1960 EQU * 

THI E3,X'10' 

BNZ TLX1970 

RHR E2,E7 

LPSWR EO 

TLX1970 EQU * 

L E5,CCB.DCB(E4) 



IS IT A NO -MOTION INTERRUPT 
YES, WRAP IT UP 
DON'T NEED THIS HALFWORD 
WAIT EOR NEXT INTERRUPT. 

GET THE DCB ADDRESS 
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LA 


£7,111 


STH 


E7,ISPTAB(E2,E2) 


OC 


E2,DCB.CDAR(E5) 


LH 


E7, DCB. TOUT (E5) 


BNP 


TLX1980 


LCS 


E6,l 


STH 


E6, DCB. TOUT (E5) 


L 


E6, DCB. LEAF (E5) 


ATL 


E6,SQ 


TLX1980 LPSWR EO 

* 


IMPUR 


TLX1990 EQU 


* 


LHL 


UCDCB.CCB(UD) 


LHL 


U6 , DCB . DN (UD) 


LH 


U8,DCB.TOUT(UD) 


BZ 


TLX2000 


BAL 


U8,TOCHOFF 


L 


UB,CCB.EB1(UC) 


LH 


U9,CCB.MISC(UC) 


THI 


U^X^OOO* 


BZR 


UB 


LHI 


U8,X'8283' 


STH 


U8, DCB. STAT (UD) 


B 


TLX2150 



SET NULL INTERRUPT 
* 

DISARM INTERRUPTS 

SEE IF WE HAVE TIMED OUT 

IF SO, DON'T ADD LEAF TO QUEUE 

RESET THE TIME-OUT VALUE 

GET THE LEAF ADDRESS 

AND ADD IT TO SYSTEM QUEUE 

AND GET ON WITH THE SHOW 



MAKE SURE THIS IS STILL O.K. 
* 

DID WE TIME-OUT? 

YES-GO SET SPECIAL STATUS. 

GET OFF THE TIME-OUT CHAIN 

RESTORE THE RETURN ADDRESS 

GET THE STATUS WE NEED 

WRITE PROTECTED ? 

NO, RETURN 

YES 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



* THE FOLLOWING CODE IS EXECUTED ON A TIMEOUT CONDITION WHICH 

* MAY OCCUR IF NO -MOTION DOES NOT SET FOLLOWING AN OUTPUT 

* COMMAND OF X ' 30 ' (SENSE DRIVE STATUS). 



TIMED OUT - SET SPECIAL STATUS 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



TLX2000 EQU * 

LHI U8,X'82DE' 
STH U8, DCB. STAT (UD) 
B TLX2150 
EJECT 

* BAL U9,TLX2050 

* THE FOLLOWING ROUTINE IS CALLED WHEN IT IS NECESSARY TO DETERMINE 

* IF WE ARE AT BOT OR EOT. THIS IS DONE AT THE START OF THE DRIVER 

* IF EOT WAS ENCOUNTERED PREVIOUSLY OR DURING THE CURRENT SENSE 

* STATUS OPERATION. THIS ROUTINE IS ALSO CALLED DURING SOME ERROR 

* ROUTINES SO THAT THE APPROPRIATE 'EOM' STATUS MAY BE SET FOR THE 

* USER. 



4-44 



48-190 FOO ROO 



TLX2050 EQU 


* 


LI 


U8 , MAGREWB 


RBT 


U8,DCB.FLG1(UD) 


LI 


U8,MAGWAT2B 


TBT 


U8,DCB.FLG1(UD) 


BNZ 


TLX2060 


SSR 


U6,UO 


THI 


UO,EOM 


BZ 


TLX2140 


TLX2060 EQU 


* 


RBT 


U8,DCB.FLG1(UD) 


ST 


U9,CCB.EBO(UC) 


LA 


U8,TLX2110 


ST 


U8,DCB.ESR(UD) 


LA 


U8 / TLX2070 


STH 


U8 , CCB . SUBA (UC) 


LA 


U8,1(UC) 


STH 


U8,ISPTAB(U6,U6) 


LIS 


U8,3 


STH 


U8,DCB.TOUT(UD) 


BAL 


U8,T0CH0N 


OC 


U6,DCB.CENB(UD) 


OC 


U6,DCB.DSBO+l(UD) 


B 


EVRTE 



REWIND BIT 

RESET IT 

ET ENCOUNTED IN PREVIOUS ACTION ? 

YES 

SENSE STATUS 

TEST BOT/EOT STATUS 

BRANCH IF NOT BOT/EOT 

RESET MAGWAT2B FLAG 
SAVE RETURN ADDRESS 
ADDRESS OF ESR FOR BOTT 
SET NEW ESR ENTRY 
SET UP EIRST BOTT ISR 
* 

MAKE ADDRESS ODD FOR CCB 
* AND SET IN ISPT 
SET A SHORT TIME-OUT 

GET ON THE TIME-OUT CHAIN 
ENABLE INTERRUPTS AND 
ISSUE SENSE COMMAND (X'30') 
EXIT FROM ESR 



* INTERRUPT SERVICE 



PURE 
TLX2070 EQU * 

LA E7,TLX2080 
STH E7, CCB. SUBA (E4) 
RH E2,CCB.MISC(E4) 
LPSWR EO 



NEXT BOTT ISR 

* MUST BE SAVED IN CCB 

READ THE HALFWORD WE NEED 

WAIT FOR BUSY TO DROP TO GIVE 

US THE NEXT INTERRUPT. 



TLX2080 EQU * 

THI E3,X'10' 

BNZ TLX2090 

RHR E2.E7 

LPSWR EO 

TLX2090 EQU * 

L E5 / CCB.DCB(E4) 

LA E7,III 



IS IT A NO-MOTION INTERRUPT 
YES, WRAP IT UP 
DON'T NEED THIS HALFWORD 
WAIT FOR NEXT INTERRUPT. 

GET THE DCB ADDRESS 
SET NULL INTERRUPT 
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STH 


E7,ISPTAB(E2,E2) 




OC 


E2 / DCB.CDAR(E5) 




LH 


E7,DCB.T0UT(E5) 




BNP 


TLX2100 




LCS 


E7,l 




STH 


E7,DCB.T0UT(E5) 




L 


E6,DCB.LEAF(E5) 




ATL 


E6,SQ 


TLX2100 


LPSWR 
IMPUR 


EO 


TLX2110 


EQU 


* 




LHL 


UCDCB.CCB(UD) 




LHL 


U6,DCB.DN(UD) 




BAL 


U8,T0CH0FF 




LH 


U8,DCB.T0UT(UD) 




BZ 


TLX2145 




L 


U9,CCB.EB0(UC) 




LH 


UO / CCB.MISC(UC) 




THI 


ucx'sooo' 




BZ 


TLX2130 




LI 


U8,MAGB0TB 




SBT 


U8,DCB.FLG1(UD) 




BR 


U9 


TLX2130 


EQU 


* 




LI 


U8 , MAGEOTB 




SBT 


U8,DCB.FLG1(UD) 




BR 


U9 


TLX2140 


EQU 


* 




LI 


U8 , MAGEOTB 




RBT 


U8,DCB.FLG1(UD) 




LI 


U8 , MAGBOTB 




RBT 


U8,DCB.FLG1(UD) 


* 


BR 


U9 


* COME HERE ONLY ON TIMEOUT 

* 


TLX2145 


EQU 


* 




LHI 


U8,X'82DF' 




STH 


U8 , DCB . STAT (UD) 



DISARM INTERRUPTS 

SEE IF WE HAVE TIMED OUT 

IF SO, DON'T ADD LEAF TO QUEUE 

SHOW SUCCESSFUL COMPLETION 

GET THE LEAF ADDRESS 

AND ADD IT TO SYSTEM QUEUE 

AND GET ON WITH THE SHOW 



MAKE SURE THIS IS STILL O.K. 
* 

GET OFF TIME-OUT CHAIN 

DID WE TIME-OUT? 

YES- GO TO ERROR EXIT 

RESTORE LINK REG (JUST IN CASE) 

GET STATUS IN UO 

BOT STATUS ? 

NO ,MUST BE EOT , BRANCH 

BOT BIT 

SET BOT FLAG 

RETURN 

CHECK EOT CONDITION 



SET EOT FLAG 
RETURN 



RESET THE EOT FLAG 

BOT BIT 

RESET BOT FLAG 

RETURN 



B TLX2150 

TITLE CONCURRENT REWIND 



YES - SET SPECIAL FLAG 
STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 
LOGIC 
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* 
* 

* 
* 
* 
* 
* 

* 

* Upon any I/O complete, check to 

* same controller is rewinding. I 

* IODONE) . If so, branch to check 



Problem: 

If a tape drive is rewinding, no I/O can be done on a 
second drive on the same controller, if an I/O request 
has been issued to the rewinding drive. 

Solution: 



see if any other drive on the 
f not, proceed normally (go to 
if the rewind is complete. 



TLX2150 


EQU 


* 




LHI 


U0,X'7FFF' 




STH 


UO,DCB.TOUT(UD) 




L 


UO,DCB.REWF(UD) 


* 


BZ 


IODONE 


* 


LIS 


U9,8 


TLX2160 
* 


EQU 


* 




L 


U1,DCB.RTBL(U9,UD) 




BZ 


TLX2180 




LH 


U2,DCB.DN(U1) 




SSR 


U2,U3 




THI 


U3,X'D1' 




BZ 


TLX2180 




LHI 


U6,X"2050' 




EPSR 


U7,U6 




LH 


U3,DCB.T0UT(U1) 




BNP 


TLX2170 




LCS 


U3,l 




STH 


U3,DCB.T0UT(U1) 




L 


U3,DCB.LEAF(U1) 




ATL 


U3,SQ 


TLX2170 


EQU 


* 




EPSR 


U6,U7 




LIS 


U3,0 




ST 


U3,DCB.RTBL(U9,UD) 



RESET TIME-OUT CONSTANT 
(THIS IS SORT OF STUPID) 
GET COMMON FLAG (FOR REWIND) 
GO TO O.S. ROUTINE FOR I/O DONE, 



INDEX INTO TABLE 



GET FIRST ENTRY IN TABLE 

NONE, HERE -- TRY NEXT 

GET ADDRESS OF REWINDING DRIVE 

WHAT IS THE STATUS? 

DID SOMETHING HAPPEN? 

STILL REWINDING- -TRY NEXT 

GO NONINTERRUPTABLE (CAN'T BE HELPED) 

GET TIMEOUT CONSTANT 
ALREADY ON QUEUE 

SET TO INDICATE ON QUEUE 

GET LEAF ADDRESS 

AND ADD TO SYSTEM QUEUE 



BECOME INTERRUPTABLE AGAIN 
ZERO ENTRY IN TABLE 
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TLX2180 


EQU 


* 




SIS 


U9,4 




BNM 


TLX2160 




L 


UO,DCB.RTBL+0(UD) 







U0 / DCB.RTBL+4(UD) 







U0,DCB.RTBL+8(UD) 


* 


ST 


UO,DCB.REWF(UD) 


* 


B 


IODONE 


* START 


ESR 




TLX2190 


EQU 


* 




LH 


U6,DCB.DN(UD) 




SSR 


U6,U3 




THI 


U3,X'D1* 




BNZ 


TLX2200 



DECREMENT INDEX 

GET FIRST ENTRY IN THE TABLE 

* ALSO INCLUDE SECOND 

* AND THE THIRD 

FIX THE FLAG TO SHOW WHETHER 

OR NOT WE STILL HAVE WORK TO DO. 

* GET OUT OF HERE 



GET ADDRESS OF REWINDING DRIVE 

WHAT IS THE STATUS? 

DID ANYTHING HAPPEN? 

IF NOT, CONTINUE PROCESSING 



* KEEP COUNT 

* DO THIS 45 

* REWIND GOT 



OF HOW MANY TIMES WE HAVE DONE THIS. IF WE 
TIMES (90 SECONDS) WE WILL ASSUME THAT THE 
KILLED BY THE OPERATOR. 



L U2,DCB.RG(UD) 

AIS U2,l 

ST U2,DCB.RG(UD) 

CHI U2,45 

BNM TLX2195 

LIS U2,2 

STH U2 / DCB.T0UT(UD) 

L UF,DCB.LEAF(UD) 

LIS UE,3 

BAL U8,EVREL 

LIS UE,2 

BAL U8,EVREL 

B EVRTE 



GO FORCE TIME-OUT 
SET 2 SECOND TIMEOUT 

GET LEAF ADDR FOR DISCONNECT 
RELEASE SELCH AGAIN 

RELEASE CONTROLLER AGAIN 
* THIS IS STUPID. 
GO BACK TO O.S. 



* COME HERE IF THE REWIND TIMES OUT. 
* 



TLX2195 



EQU 
LHI 
STH 
B 



U8,X'8277' 

U8,DCB.STAT(UD) 

TLX2150 



SET INDICATOR 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 
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TLX2200 EQU * 

LA U8,III 

STH U8,ISPTAB(U6,U6) 

OC U6,DCB.CDAR(UD) 

LHL UCDCB.CCB(UD) 

LHI U7 , X * 7FFF ' 

STH U7,DCB.TOUT(UD) 

BAL U8,T0CH0FF 

LI U8 / MAGREWB 

RBT U8 , DCB.. FLG1 (UD) 

* NOW DO REWIND BOOKKEEPING 
LIS U3,0 



TLX2210 



TLX2220 



TLX2230 



TLX2240 



LIS 

EQU 

L 

BZ 

LIS 

EQU 

C 

BNE 

ST 

EQU 

SIS 

BNM 

L 





ST 

EQU 

SIS 

BNM 

B 



U7,8 

* 

U2 , DCB . XDRV (U7 , UD) 

TLX2240 

U8,8 

* 

UD,DCB.RTBL(U8,U2) 

TLX2230 

U3,DCB.RTBL(U8,U2) 

U8,4 

TLX2220 

U3,DCB.RTBL+0(U2) 

U3,DCB.RTBL+4(U2) 

U3,DCB.RTBL+8(U2) 

U3,DCB.REWF(U2) 
* 

U7,4 

TLX2210 

TLX0018 



CLEAR ISPT 

DISARM INTERRUPTS FROM DRIVE 

RELOAD CCB ADDRESS 

NO TIME-OUT 



RESET THE REWINDING FLAG 



SET UP ZERO FOR STORAGE IN TABLE 
SET UP COUNTER 

GET DCB ADDRESS OF ANOTHER DRIVE 
TRY ANOTHER SLOT 
SET UP INNER INDEX 

IS THIS OUR ADDRESS? 
NO, IGNORE IT 
ZERO THE ENTRY 

DECREMENT INNER INDEX 
LOOP AGAIN 

GET DCB ADDRESS 

* 

* 
* 

DECREMENT OUTER INDEX 

LOOP AGAIN 

RETURN TO MAINLINE CODE 



* COME HERE IF EX OR DU IS SET ON 

* STATUS IS IN REGISTER U7. 
* 



TLX2250 EQU 


* 


THI 


U7,X'FO' 


BNZ 


TLX2255 


LI 


UO,MAGREWB 


TBT 


UO,DCB.FLGl(UD) 


BNZ 


TLX0015 


LHI 


U8,X'AOOO' 



ENTRY TO THE DRIVER. 



ERR, TERR, EOM, NMTN SET? 

IF SO, BRANCH TO DO NEXT TEST 

GET REWIND FLAG BIT 

IS IT SET? 

IF REWIND FLAG IS SET, GO BACK 

OTHERWISE, REPORT DEV UNAVAIL. 
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STH 


U8, DCB. STAT (UD) 




B 


TLX2150 


TLX2255 


EQU 


* 




THI 


U7,DU 




BZ 


TLX0015 




LHI 


US^'AOOO' 




STH 


U8, DCB. STAT (U D) 




B 


TLX2150 



STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 

IS DU STATUS SET? 

IF NOT, CONTINUE PROCESSING 

IF DU SET, GIVE ERROR CODE 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



* COME HERE IF WE HAVE ISSUED AN I/O REQUEST TO A DRIVE 

* THAT WE BELIEVE TO BE CURRENTLY REWINDING. 
* 

TLX2260 EQU * 

* 



IF THE I/O REQUEST IS A BSR OR BFM, TERMINATE THE I/O 

REQUEST WITH A STATUS OF '9000'. 

IF THE I/O REQUEST IS A REWIND, SET THE STATUS TO ZERO AND EXIT 



GET THE SVC 1 FUNCTION CODE 

BACK FILE MARK? 

IF SO, EXIT 

BACK SPACE RECORD? 

IF SO, EXIT 

IS IT REWIND? 



LB 


U3,DCB.FC(UD) 


CHI 


U3,X'82' 


BE 


TLX2345 


CHI 


US^'AO 1 


BE 


TLX2345 


CHI 


U3 , X ' CO ' 


BE 


IODONE 



SET A COUNTER TO TIME-OUT THE REWIND. 





LIS 


U3,0 




ST 


U3,DCB.RG(UD) 




LIS 


U3,8 


TLX2270 


EQU 


* 




L 


U8,DCB.XDRV(U3,UD) 




BZ 


TLX2300 




LIS 


U9,0 


TLX2280 


EQU 


* 




L 


U7,DCB.RTBL(U9,U8) 




BNZ 


TLX2290 




ST 


UD,DCB.RTBL(U9,U8) 




ST 


UD,DCB.REWF(U8) 




B 


TLX2300 


TLX2290 


EQU 


* 




AIS 


U9,4 



(SEE ALSO TLX2190) 
SET OUTER INDEX 

GET DCB ADDRESS 
IGNORE IF NOT PRESENT 
SET INNER INDEX 

GET ENTRY IN OTHER DCB TABLE 
THIS SLOT ALREADY USED 
SAVE OUR ADDRESS HERE 
SET REWIND FLAG 
DONE WITH THIS DCB 

I NCR INNER INDEX 
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CHI 


U9,12 




BM 


TLX2280 


TLX2300 


EQU 


* 




SIS 


U3,4 




BNM 


TLX2270 




LA 


UE / TLX2190 




ST 


UE,DCB.ESR(UD) 




LIS 


UE,3 




L 


UF, DCB. LEAF (UD) 




BAL 


U8,EVREL 




LIS 


UE,2 


* 


BAL 


U8,EVREL 




LA 


U7,TLX2310 




STH 


U7,CCB.SUBA(UC) 




LA 


U7,1(UC) 




STH 


U7,ISPTAB(U6,U6) 




BAL 


U8 , TOCHON 




LIS 


U7,l 




STH 


U7, DCB. TOUT (UD) 




OC 


U6,DCB.CENB(UD) 




B 


EVRTE 




PURE 




TLX2310 


EQU 


* 




THI 


E3,NMTN!DU 




BZ 


TLX2330 




L 


E5 / CCB.DCB(E4) 




L 


E6, DCB. LEAF (E5) 




LH 


E7, DCB. TOUT (E5) 




BNP 


TLX2330 




LCS 


E7,l 




STH 


E7, DCB. TOUT (E5) 




ATL 


E6,SQ 


TLX2330 


EQU 


* 




LPSWR 


EO 




TITLE 


ERROR ROUTINES 


* ERROR 

* 


HANDLING SUBROUTINES 




IMPUR 




TLX2340 


EQU 


* 




LI 


U8,X'A000' 




STH 


U8 , DCB . STAT (UD) 




B 


TLX2150 



DONE YET? 

LOOP UNTIL DONE 

DECR OUTER INDEX 

LOOP UNTIL DONE 

ADDRESS OF ESR 

SET UP FOR NEXT ESR SCHEDULING 

RELEASE SELCH 

GET LEAF. ADDRESS 

* 

RELEASE CONTROLLER 

ISR ADDRESS 
* AND SAVE IT 
ODD CCB ADDRESS 
* 

GET ON TIMER CHAIN 



ENABLE DRIVE INTERRUPTS 



NO -MOTION OR DU? 
YES, SCHEDULE ESR . 
GET DCB ADDRESS 
AND LEAF ADDRESS 
HAVE WE TIMED OUT? 
GET OUT OF HERE IF SO 
SET TIME OUT TO - 1 
* 

SCHEDULE ESR 
GET OUT 



DU STATUS 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 
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TLX2345 


EQU 






LHI 


us, x' 9000 ■ 




STH 


U8, DCB. STAT (UD) 




B 


TLX2150 


TLX2350 


EQU 


* 




LI 


U8 , X ' 8400 ' 




STH 


U8,DCB.STAT(UD) 




B 


TLX2150 


TLX2360 


EQU 


* 




LI 


us^'cooo* 




STH 


U8, DCB. STAT (UD) 


* 


B 


TLX2150 


TLX2370 


EQU 


* 




BAL 


U7 , TLX2400 




OHI 


U8,X'84FB' 




STH 


U8, DCB. STAT (UD) 




B 


TLX2150 



EOM STATUS 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 

UNRECOVERABLE ERROR 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 

ILLEGAL FUNCTION STATUS 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



IS IT THE END OF TAPE CASE ? 

SET UP STATUS CODE 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



TLX2380 EQU * 

BAL U7,TLX2400 

STH U8 , DCB . STAT (UD) 

B TLX2150 



IS IT THE END OF TAPE CASE ? 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



TLX2390 EQU * 

BAL U7,TLX2400 
OHI U8,X'82FA' 
STH U8 , DCB . STAT (UD) 

B TLX2150 



IS IT AT THE END OF TAPE ? 

SET UP RECOVERABLE STATUS 

STORE STATUS 

CHECK FOR REWIND IN PROGRESS & EXIT. 



* 
* 

4 


BAL 


U7 , TLX2400 




TLX2400 


EQU 


* 






BAL 


U9,TLX2050 






LIS 


U8,0 


CLEAR U8 




LI 


U9 , MAGE OTB 


EOT FLAG SET ? 




TBT 


U9,DCB.FLG1(UD) 






BZR 


U7 


NO, RETURN 




RBT 


U9,DCB.FLG1(UD) 


RESET EOT FLAG 




LHI 


us^'gooo 1 


REPORT EOT STATUS 




BR 


U7 


RETURN 



TITLE TELEX I/O HANDLERS 
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* BUILD IOH LIST FOR COMMON SVC1 EXECUTORS 



ALIGN 


4 


IOH 


NAME=IOHTELX, 




READ=TLX2450, 




WRITE=TLX2460, 




WAIT=SVC1WAIT, 




HALT=SVC1HALT, 




TEST=SVC1TEST, 




SET=SVC1N00P , 




REW=SVC1REW, 




BSR=SVC1BSR, 




FSR=SVC1FSR, 




WFM=SVC1WFM, 




FFM=SVC1FFM, 




BFM=SVC1BFM, 




INIT=TLX2490, 




DDF=TLX2420 


TLX2420 EQU 


* 


ST 


EA, TLX2470 


ST 


EB,TLX2480 


LB 


EA, I0B.SV1X+3(EA) 


CHI 


EA,8 


BE 


TLX2430 


CHI 


EA,10 


BE 


TLX2430 


L 


EA, TLX2470 


B 


SVC1DDF 


TLX2430 EQU 


* 


L 


EA, SVC1 . SAD (ED) 


THI 


EA, 1 


BNZ 


TLX2440 


L 


EB,SVC1.EAD(ED) 


BAL 


E8,ADCHKNS 


BC 


TLX2440 


LR 


EC,EA 


L 


EA,TLX2470 


ST 


ECIOB.SADR(EA) 


ST 


EB,IOB.EADR(EA) 


L 


EB,TLX2480 


B 


SVC1BFM 


SPACE 




TLX2440 EQU 


* 



SAVE I OB ADDRESS 

SAVE DCB ADDRESS 

GET EXTENDED SVC1 WORD 

ADDRESS CHECKING REQUIRED ? 

YES, BRANCH 

CHECK BUFFER ON ERASE BUFFER 

* FUNCTION. 

RESTORE IOB ADDRESS 

GO TO ROUTINE TO ENTER DRIVER 

GET START AND END ADDRESSES 



FOR ADDRESS CHECKING ROUTINE 

CHECK ADDRESSES 

ADDRESS ERROR, EXIT 

SAVE RELOCATED SADR 

RESTORE IOB ADDRESS 

STORE RELOCATED START AND 

END ADDRESSES 

RESTORE DCB ADDRESS 

GO TO ROUTINE TO ENTER DRIVER 



1 
1 

1 
1 
1 
1 
1 
1 
1 
1 
1 
1 
1 
1 
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L 


EA, TLX2470 




RELIOB REMW=NO 




L 


EA,TCB.SAVE(E9) 




LM 


EE,CTX.PSW(EA) 




B 


MEMFAULT 


TLX2450 


EQU 


* 




L 


ECIOB.SADR(EA) 




SRLS 


EC,1 




BNC 


SVC1READ 




B 


TLX2440 


TLX2460 


EQU 


* 




L 


ECIOB.SADR(EA) 




SRLS 


EC,1 




BNC 


SVC1WRIT 




B 


TLX2440 




SPACE 






ALIGN 


4 


TLX2470 


DCF 





TLX2480 


DCF 







ALIGN 


4 


TLX2490 


EQU 


* 


* 







RESTORE I OB ADDRESS 

RESTORE REGISTERS 

GO TO ERROR ROUTINE 

FETCH START ADDRESS 

EVEN ? 

YES, CONTINUE 

NO, ERROR EXIT 

FETCH START ADDRESS 

EVEN ? 

YES, CONTINUE 

NO, ERROR EXIT 



I OB ADDRESS SAVE AREA 
DCB ADDRESS SAVE AREA 



UB CONTAINS THE DCB ADDRESS UPON ENTRY 



TLX2500 



TLX2510 



L 


UD, DCB. LEAF (UB) 


L 


UD,EVN.CORD(UD) 


LIS 


UC,0 


LA 


UE,DMT 


EQU 


* 


L 


U9,4(UE) 


BZR 


U8 


BM 


TLX2510 


CR 


UB,U9 


BE 


TLX2510 


L 


UA, DCB. LEAF (U9) 


C 


UD,EVN.CORD(UA) 


BNE 


TLX2510 


ST 


U9 , DCB . XDRV (UC , UB) 


AIS 


UC,4 


EQU 


* 



GET THE LEAF ADDRESS 

GET UPPER NODE (COMMON POINT 

FOR DRIVES ON THE SAME CONTROLLER. 

INDEX INTO TABLE 

GET ADDRESS OF DMT 

GET FIRST DCB ADDRESS 
RETURN TO SYSINIT. 
IGNORE PSEUDO DEVICES 
IGNORE OURSELF 

AND OBTAIN LEAF ADDRESS 

AND THEN CORD. 

GET NEXT ENTRY 

SAVE THIS DRIVE'S ADDRESS 



init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
init 
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TLX2520 



TLX2530 



TLX2540 



TLX2550 



TLX2570 



TLX2580 



AIS 


UE,8 




GET NEXT DMT ENTRY 


B 


TLX2500 






TITLE 


MAG DENSITY 


SELECTION 


EQU 


* 






LA 


U3,TLX2600 






LB 


U1,SVC7.0PT+1(U5) 




NHI 


Ul,7 




DENSITY SELECTED? 


BZ 


TLX2530 




NO 


LA 


U3,TLX2600 






CLHI 


U1,S7.800 




800 BPI SELECTED? 


BNE 


TLX2540 




NO 


LB 


U3,0(U3) 






B 


TLX2580 






SPACE 


1 






EQU 


* 






LB 


U3,3(U3) 






B 


TLX2580 






SPACE 


1 






EQU 


* 






CLHI 


U1,S7.1600 




1600 BPI SELECTED? 


BNE 


TLX2550 




NO 


LB 


U3,1(U3) 






B 


TLX2580 






SPACE 


1 






EQU 


* 






CLHI 


U1,S7.6250 




6250 BPI SELECTED? 


BE 


TLX2570 




YEP 


SPACE 


1 






LR 


U8,U8 




SET CC=NONO 


BR 


U8 




RETURN 


SPACE 


1 






EQU 


* 






LB 


U3,2(U3) 






SPACE 


1 






EQU 


* 






LB 


U1,DCB.DENS 


(U7) 




NHI 


Ul , X * CF ' 






OR 


U1,U3 




SET NEW DENSITY 


STB 


U1,DCB.DENS 


(U7) 




SPACE 


1 






LB 


U1,DCB.CENB 


(U7) 




NHI 


Ul , X ' CF ' 






OR 


U1,U3 




SET NEW DENSITY 



init 
init 
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STB 


U1,DCB.CENB(U7) 






SPACE 


1 






LB 


U1,DCB.CDAB(U7) 






NHI 


Ul , X ' CF ' 






OR 


U1,U3 






STB 


U1,DCB.CDAB(U7) 






SPACE 


1 






LB 


U1,DCB.CDAR(U7) 






NHI 


U1,X'CF' 






OR 


U1,U3 . 






STB 


U1,DCB.CDAR(U7) 






SPACE 


1 






LB 


U1,DCB.CCLC(U7) 






NHI 


Ul , X ' CF ' 






OR 


U1,U3 






STB 


U1,DCB.CCLC(U7) 






SPACE 


1 






LB 


U1,DCB.CGPL(U7) 






NHI 


U1,X'CF* 






OR 


U1,U3 






STB 


U1,DCB.CGPL(U7) 






SPACE 


1 


* 




OC 


U1,DCB.DSB3(U7) 


* 
* 




RH 


U1,DCB.STA3(U7) 


* 

■k 


STAT CHECKS ( 


DUT: 


* 


OK 


- RETURN CC=0 


* 


NG 


- RETURN CC=NONO 






SPACE 


1 






XAR 


U1.U1 






BR 


U8 






SPACE 








ALIGN 


ADC 


TLX2600 


EQU 


* 






DB 


X'20' 






DB 


X'OO* 






DB 


X'lO 1 






DB 


X'30' 






ALIGN 


ADC 






BR 


UB 


SI 


ZE 


EQU 


IMPTOP-TLX0010+7/8 



SET NEW DENSITY 



SET NEW DENSITY 



SET NEW DENSITY 



SET NEW DENSITY 



READ STATUS FOR DENSITY 



SET CC=0 

GO HOME FOR NOW ! 



800 BPI - TELEX & STC 

1600 BPI 

6250 BPI 

HARDWARE SELECT (TELEX ONLY) 

EXIT 
*8+PURET0P-TLX0360+7/8*8 
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END 
**DCB070 

NLSTC 

MLIBS 8,9,10 
SGN.MAGS EQU 1 
SGN.EOV EQU 1 

NLIST 

DPROG DC0D=070 

LIST 

$MTP 
* 



USED BY $MTP MACRO 



CCB 



SELCH 



* BUILD DCB FOR TELEX/6250/HALFWORD MODE 
* 

DCB DC0D=070,INIT=INITTELX,TERM=TERMTELX, 1 

ATRB=7BFF,SIZE=MTP,CLASS=I0CLS1, 1 

FUNC=CMDTELX, FLGS=DFLG.UCM+DFLG.LNM+DFLG.MGM, IOH=IOHTELX 

* DEVICE DEPENDENT 

EXTRN Z(CDN2) 

ORG DCBO 7 + DCB . CCB 

DC Z(CCB070) 

ORG DCB070+DCB . SDN 

DC Z(CDN2) 

ORG DCB070+DCB . SADR 

EXTRN INITSUBS 

DAC INITSUBS 

EXTRN INITMAGS 

DAC INITMAGS 

ORG DCB070+DCB.DENS 

DB X'38' 

ORG DCB070+DCB.CENB 

DB X'78' 

ORG DCB070+DCB . CDAB 

DB X ' B8 ' 

ORG DCB070+DCB . CDAR 

DB X'FS' 

ORG DCB070+DCB.CCLC 

DB X'39' 

ORG DCB070+DCB . CCLD 

DB X ' 10 ' 

ORG DCB070+DCB.CRDF 

DB X ' 40 ' 

ORG DCB070+DCB.CRDB 



SUBROUTINES 



Allow drive to select density. 



ENABLE INTERRUPTS 



DISABLE INTERRUPTS 



DISARM INTERRUPTS 



CLEAR CONTROLLER 



CLEAR DRIVE 



READ FORWARD 



48-190 FOO ROO 



4-57 



DB X ' 50 ' 

ORG DCB070+DCB.CWRT 

DB X ' 60 ' 

ORG DCB070+DCB . CREW 

DB X'EO' 

ORG DCB070+DCB.CBSR 

DB X ' 90 ' 

ORG DCB070+DCB.CFSR 

DB X ' BO ' 

ORG DCB070+.DCB.CWFM 

DB X ' CO ' 

ORG DCB070+DCB.CFFM 

DB X'AO' 

ORG DCB070+DCB.CBFM 

DB X ' 80 ' 

ORG DCB070+DCB.CERS 

DB X'DO' 

ORG DCB070+DCB . CLWR 

DB X ' 70 ' 

ORG DCB070+DCB.CUNL 

DB X'FO' 

ORG DCB070+DCB.CGPL 

DB X'7A' 

ORG DCB070+DCB . CNOP 

DB 

ORG DCB070+DCB.CDDF 

DB 

ORG DCB070+DCB.CNFD 

DB 

ORG DCB070+DCB.DSB0 

DCX 0030,0131,0232,0333 

ORG DCB070+DCB . BPG 

DC 5600,21875,2800 

ORG DCB070+DCB . SPED 

DC H'125' 

ORG DCB070+DCB.RATE 

DC *-* 

ORG DCB070+DCB.XRT 

DC 200000,781250,100000 

* SET UP A TIMEOUT CONSTANT FOR USE 

ORG DCB070+DCB.MAXT 

DC X'20* 

* READ AND WRITE RETRY COUNTS 



READ BACKWARD 

WRITE A BLOCK 

REWIND 

BSR 

FSR 

WFM 

FFM 

BFM 

ERASE GAP 

LOOP WRITE TO READ 
TLX1700 REWIND 

GAPLESS INTERRUPT ENABLE 

NO-OPERATION 

DEVICE -DEPENDENT 

COMMAND NOT FOUND 

NOP AND TAPE UNIT SENSE 

BYTES PER GAP 

PE, GCR, NRZI 

DRIVE SPEED (INCHES/SECOND) 

DATA TRANSFER RATE (BYTES/SECOND) 

DATA TRANSFER RATES 

IN SOME OPERATIONS 
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ORG 


DCB070+DCB. 


,RRTY 


DC 


X'07 1 




ORG 


DCB070+DCB, 


,WRY1 


DC 


X'07* 




ORG 


DCB070+DCB, 


,WRY2 


DC 


X'07' 




ORG 


DCB070+MTP 





* BUILD CCB FOR 6250 BPI MAG TAPE 
CCB DC0D=07O 
END 
BEND 



SYSGEN3 



%RQU 

%MDN 

%MCNT 

%MSLCH 

%CCBFL 

%CLASN 
&CLSNTD 



2 DCB macro for Telex tape driver: 
MACRO 

DCB249 %DCOD= , %DN= , %CLAS= , %ILVL= , %NAME= , 
%SLCH= , %CNTR= , %SHCCB= , %EOV=0 
%DCB$ , %PDCB , %DDCB , %EVN , %CCB , %DFLG, %SDCB 
%IDCB, %ODCB, %S125DCB, %ICCB, %BDCB 
%ADCB, %TCB, %IOB, %IOB$ , %CRTDCB , %LPDCB 
%MMDDX , %DDEX , %VFDCB , %CRPDCB , %MGDCBX , %HF WDST 
%PSDCBX, %CRDP , %AOBDCB, %BI0CDCB, %LPTDCB 
%MTPT 
%IDVAL 
BGBLA %ID249 
LCLA %CCBFL 
%CLASN 
%RXLT,%RQU 
%CORDNM, %PTRPAS 
%OFFS 
%RDN 

%MDN , %MCNT . %MSLCH 
%TRCNT,%UPTR 
%FOUND,%DA 
BGBLA %FIRST 

SETC 'COMQ' DEFAULT DEVICE QHANDLER 

'%DN' DEVICE ADDRESS 

' %CNTR ' CONTROLLER 

'%SLCH' SELCH 



(T'%CLAS EQ 'U*)&CLSNTD 
%CLAS*12 I0CLASS*12 



GBLB 
GBLB 
GBLB 
GBLB 
GBLB 
GBLB 
GBLC 



LCLA 
LCLC 
LCLC 
LCLC 
LCLA 
LCLC 
LCLA 
LCLB 



SETC 

SETC 

SETC 

SETA 

AIF 

SETA 

ANOP 
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CONVNUM VAL=%ID249 CONVERT CURRENT ID TO HEX. 

USERINIT 



SGN, 


.MAGS EQU 


SGN, 


.TELX EQU 1 


SGN, 


.EOV EQU 1 




$DCB$ 




DCBI D 



DC0D=249,SIZE=MTPT,INIT=INITTELX,I0C=1, 1 

TERM=TERMTELX, FLGS=DFLG.UCM+DFLG.LNM+DFLG.MGM, 2 

FUNC=CMDTELX , I D=%I DVAL , ATRB=7BFF , COPY=$MTPT , 3 

SADR-INITSUBS , I OH=I OHTELX 

ORG DCB%DCOD%IDVAL+DCB . SADR+4 

EXTRN INITMAGS 

DAC INITMAGS 

TMTPI DCOD=249,ID=%IDVAL,DENS=38,CENB=78,CDAB=B8,CDAR=F8, 1 
CCLC=39 , CCLD=10 , CRDB=50 , CWRT=60 / CREW=EO , CBSR=90 , 2 
CFSR=BO , CWFM=CO , CFFM=AO , CBFM=80 , CERS=DO , CC0N=7E , SPED=1 25 

ORG DCB%DCOD%IDVAL+DCB.DSBO 

DCX 0030,0131,0232,0333 NOP AND TAPE UNIT SENSE 

ORG DCB%DCOD%IDVAL+DCB.BPG BYTES PER GAP 

DC 5600,21875,2800 NRZI , PE, GCR 

ORG DCB%DCOD%IDVAL+DCB.XRT MAX BUFFER SIZE FOR ERASE TAPE 

DC 200000,781250,1000000 NRZI, GCR, PE 

ORG DCB%DCOD%IDVAL+DCB.CUNL 

DB X'FO' 

ORG DCB%DCOD%IDVAL+DCB.CGPL 

DB X'7A* 

CCBI DC0D=249,ID=%IDVAL 
CCB%NAME EQU CCB%DCOD%IDVAL 
%ID249 SETA %ID249+1 
&DCBOPT ANOP 

DCB%DCOD%IDVAL PROG USER DCB 

%OFFS SETC '%DCOD* : '%IDVAL' ESTABLISH PROPER OFFSET 
DCB.%NAME EQU DCB%OFFS 

ENTRY DCB.%NAME 

ORG DCB%OFFS+DCB.DN DEVICE ADDRESS 

DC H'%DN' 

ORG DCB%OFFS+DCB.LEAF LEAF POINTER 

AIF (T'JSSHCCB' EQ 'U')&NSLEAF B IF NOT SHARED 

DAC LF%SHCCB USE SHARED DEVICE LEAF 

EXTRN LF%SHCCB 

AGO &NRMLFX 
&NSLEAF ANOP 

DAC LF%OFFS GENERATE STANDARD LEAF NAME 
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EXTRN 


LF%OFFS 


&NRMLFX 


ANOP 




&NOLEAF 


ANOP 






AIF 


(T'%CLAS EQ 'U')&NOCLAS 




ORG 


DCB%OFFS+DCB.CLAS 10 CLASS 




DC 


H*%CLASN' I0CLASS*12 


&NOCLAS 


ANOP 






AIF 


(T'%ILVL EQ 'U')&NOILVL 




ORG 


DCB%OFFS+DCB.ILVL LEVEL 




DC 


H'%ILVL* 


&NOILVL 


ANOP 






ORG 


DCB%OFFS+DCB.DMT 




DC 


DMT.%NAME A (DMT ENTRY) 




EXTRN 


DMT.%NAME 


&SKP 


ANOP 






AIF 


(T'%SLCH EQ 'U'J&NOSLCH 




ORG 


DCB%OFFS+DCB.SDN SELCH 




DCX 


%SLCH 


&NOSLCH 


ANOP 






AIE 


(T'%CNTR EQ 'U')&NOCNTR 




ORG 


DCB%OFFS+DCB.CDN CONTROLLER 




DCX 


%CNTR 


&NOCNTR 


ANOP 






AIF 


( ' %RQU ' EQ ' * ) &NOQU 




ORG 


DCB%OFFS+DCB.Q 




DAC 


%RQU 




EXTRN 


%RQU 


&NOQU 


ANOP 






ORG 


DCB%OFFS+DCB.MAXT 




DC 


X'20* 




ORG 


DCB%OFFS+DCB . RRTY 




DC 


X'07' 




ORG 


DCB%OF F S + DCB . WRY1 




DC 


X'07' 




ORG 


DCB%OFFS+DCB . WRY2 




DC 


X'07' 




ORG 


$ST%OFFS ORG TO END OF 




ASIS 






END 




%RDN 


SETA 
MEND 


%DN+1 
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CHAPTER 5 
ADVANCED DRIVER CONCEPTS 



5.1 INTRODUCTION 

As drivers evolve to handle more complicated situations, comprehension of more advanced driver 
concepts becomes necessary. Advanced concepts include the use of a translation table, which is a 
necessary driver component when the character set has to be translated from ASCII to EBCDIC or 
vice versa. The translation table is also used for recognizing special characters of communications 
protocols. Another advanced driver concept is that of the nonphysical device. Sometimes drivers 
are designed for a device that does not actually exist in order to satisfy particular design 
requirements without having to modify the operating system. The last advanced driver concept to 
be discussed in this chapter is the supervisor call 6 (SVC6) and trap generating device driver, a 
driver that is desirable in certain system configurations. 

5.2 THE TRANSLATION TABLE 

Some devices use a data code that must be converted in order to be used by other software in the 
system. For example, some card readers transmit a Hollerith code, which must be converted to 
ACSCII code to be meaningful. Interactive terminals (CRTs) can transmit special characters to 
signify that special processing is to be done, rather than have those characters be treated as data. 
CRTs use a variation of ASCII code for some special characters. The translation table is the 
mechanism provided to allow the writer of an input/output (I/O) driver to efficiently handle these 
special conditions. 

5.2.1 The TLATE Instruction 

Translation tables are processed by either the autodriver channel microcode routines or by the 
TLATE instruction. Typically, a driver accesses the translate table by both methods. The decision to 
use a translation table through the autodriver channel or via the TLATE instruction is dictated by 
the interrupt response characteristics of the specific device hardware. For example, a card reader 
typically begins generating character interrupts as soon as it is given a "go" command; thus, only the 
autodriver mechanism need be used. However, the Perkin-Elmer RS-232 interface requires that a 
single character be written to it before it generates character interrupts that can be used to drive the 
autodriver channel. Thus, for the RS-232 interface, the first character must be output via the 
TLATE and WD (WRITE DATA) instructions, while the remaining characters can be output using 
the autodriver channel. 

5.2.2 Function and Design of a Translation Table 

A translation table is structured as a list of 256 halfwords. One halfword entry corresponds to each 
possible value of an 8-bit character code. Bit of each halfword entry specifies the interpretation 
that is to be made of the remaining IS bits of that entry. If bit is set, then the least significant byte 
contains the value that is to be substituted for the original character code. If bit is zero, then bits 
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1 through 15 provide the address, divided by two, of a routine that is to be executed when the 
corresponding character code is encountered. In this case, an unconditional branch is taken to the 
indicated address. Note that this scheme requires that at least the first instruction of the special 
routine be in the first 65K of address space, since only halfword addresses can be specified. 

To illustrate how a translation table can be used, let us write a simple driver for a hypothetical 
device that requires use of a translation table for efficient operation. To keep the example to a 
manageable size, assume that this device has some rather unusual characteristics. 

We will assume that this device: 

• is a transmit-only device (we can only read from it), 

. transmits only the 8-bit codes X'08' thru X*23\ 

. the 8-bit codes X'OA' through X'23' are to be interpreted as the ASCII characters A thru Z, 

. the device begins all transmissions with the code X'08\ followed by one character that indicates 

the number of characters to follow, plus 10, 
. the device may, for undisclosed reasons, prematurely terminate a transmission with an X'09' 

code. 

First, a translation table for this strange device must be designed. Notice what only codes X*08' 
through X'23' are valid, and that codes X'08' and X*09' are special codes that indicate that special 
processing action is required. Common Assembly Language/32 (CAL/32) conveniently provides a 
special data type for setting up addresses in translation tables: 



TABLE 



EQU 


* 


DO 


8 


DC 


T (ILLEGAL) 


DC 


T (START) 


DC 


T (STOP) 


DC 


X'SOOO'+C'A' 



codes X'OO' thru X'07 1 illegal 

code X'08' = start of xfer 
code X'09" = end of xfer 
code X'lO' = letter A 



DC X'SOOO'+C'Z' code X'23' = letter Z 

DO 256-35 

DC T (ILLEGAL) all other codes are illegal 



5.2.3 Driver Code for the Translation Table 

With this table defined, a driver can now be written to drive the device. Since we have assumed that 
the device has hardware characteristics that are convenient for writing software, the driver in this 
example is simpler than it probably would be for a real device. (Compare this code to that of the 
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"read" side of the Perkin-Elmer CRT driver!) We will code this driver so that all character handling 
is done in interrupt service. Clearly, three special routines are needed: start of transmission, end of 
transmission and illegal transmission. 

For the purposes of this example, we will ignore some necessary details, such as what to do about 
time-out conditions and bad device status. The intent of this example is to show only the code 
concerned with the use of the translation table. We will pick up the code at the end of the driver 
initialization routine (DIR) part of the driver: 



INITXX 



EQU 



DIR 



enter first ISR to start device 
exit to wait for I/O completion 

come here on SINT command from DIR 

set up channel control block (CCB) for nonexecute 

set up address of next ISR 

send command to device to enable it 
exit to wait for first interrupt 

first device interrupt comes here 
get input character into register 7 
is this a start of xfer character? 
if not, it must be illegal 

Notice that at this point, we can determine what is a legal input simply by the time sequence: we 
demand that the first character received after the enable command is given must be a X'08\ 





SINT 


R5,0(R6) 


■k 


B 


DIRDONE 


ISRO 


EQU 


* 




LIS 


E7,0 




STH 


E7,CCB.CCW(E4) 




LA 


E7,ISR1 




STH 


E7,CCB.SUBA(E4) 




OC 


E2, ENABLE 


A 


LPSWR 


EO 


I SRI 


EQU 


* 




RDR 


E2,E7 




CHI 


E7 / X'08' 




BNE 


ILLEGAL 
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LA E7,ISR2 

STH E7 / CCB.SUBA(E4) 

LPSWR EO 



* 






ISR2 


EQU 


* 




RDR 


E2,E7 




SIS 


E7,10 



L 


E5,CCB.DCB(E4) 


L 


E6,DCB.SADR(E5) 


AR 


E6,E7 


SIS 


E6,l 


ST 


E6 / CCB.EB0(E4) 


LIS 


E6,0 


SIS 


E7,l 


SR 


E6,E7 


STH 


E6,CCB.LB0(E4) 


LHI 


E6,X'0082' 


STH 


E6,CCB.CCW(E4) 


LA 


E 7, TABLE 


ST 


E7,CCB.XLT(E4) 


LA 


E7,ISR3 


STH 


E7,CCB.SUBA(E4) 


LPSWR 


EO 



set up to receive next character 
this will be character count 
wait for next character 

second device interrupt comes here 
get input character into reg 7 
this is character count, plus 10 
(because we said that ' s how this 
strange device works!) 

get device control block (DCB) address, 
and compute xfer end address for 
insertion into the CCB. . . 
(adjust for inclusive addressing) 
set end addr as buffer address 
buffer count must be - ( length- 1) 
this is (length-1) 
this is - (length-1) 
finally got the buffer length set 
set up the channel command word (CCW) 
* 

get address of translate table 
and put in CCB 

get address of routine to go to 
if xfer terminates normally 
exit, and let autodriver channel 
do the rest of the work. 



(The data transfer, with translation of character values, proceeds under control of the autodriver 
channel, as defined by the values in the CCB. There are three possible exits from autodriver 
operation: to ISR3, to ILLEGAL or to STOP. All of these routines are ISRs.) 
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ISR3 EQU * 

L E5,CCB.DCB(E4) 

LIS E6,0 

STH E6, DCB. STAT (E5) 

L E7,CCB.EB0(E4) 

S E7,DCB.SADR(E5) 

AIS E7,l 

ISR3A ST E7,DCB.LXFR(E5) 

OC E 2, DISABLE 

LA £7,111 

STH E7,ISPTAB(E2,E2) 

L E7, DCB. LEAF (E5) 

ATL E7,SQ 

LPSWR EO 



enter this routine if xfer is normal 

get DCB address 

set normal termination status 

compute actual length of xfer... 



turn off the device 
and reset the ISPTAB 

finally, schedule the ESR 

on the system queue 

and exit interrupt service 



ILLEGAL 
* 



EQU 

L 

LHI 

STH 



E5,CCB.DCB(E4) 

E6,X'8484' 

E6, DCB. STAT (E5) 



LIS E7,0 



B 



ISR3A 



control will come here if 

an illegal input is encountered 

get DBC address 

designer ' s choice - indicate 

a bad character was received, 

by setting X'8484' in status 

again design choice - show 

zero length of transfer 

go to common exit 



autodriver will come here 

if device sends a "stop" code 

get DCB address 

design choice - we show this 

status if we get a stop code 

compute actual length of xfer... 

(this is actual end addr +1) 
less start address 

(arithmetic adjustment) 
go to common exit 

Notice that we have defined only two of the three "special routines" defined in the translation table. 
The "START" routine was rendered unnecessary, due to the way that the ISRs were designed. Thus, 
if the "start" code was received at any other time, it would be an "illegal" code. The definition of the 
"START" routine may be handled simply as: 



STOP 


EQU 


* 




L 


E5,CCB.DCB(E4) 




LHI 


E7,X'8201' 




STH 


E7, DCB. STAT (E5) 




LH 


E7,CCB.LB0(E4) 




A 


E7,CCB.EB0(E4) 




S 


E7,DCB.SADR(E5) 




SIS 


E7,2 




B 


ISR3A 



START EQU 



ILLEGAL 
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Probably, the greatest mystery in the above code to the first-time reader is the fact that nowhere 
was there any executable code written that explicitly invoked the operation of the autodriver channel 
and the use of the translation table. Actually, the autodriver channel was enabled by the value 
X'8002', which was stored into the CCB.CCW. That same value, plus the address of the translation 
table being placed in CCB.XLT, told the autodriver channel to use the translation table that we 
wrote. The actual operation of the autodriver channel occurred in response to interrupts generated 
by the device. 

5.3 NONPHYSICAL DEVICE DRIVERS 

In some circumstances, it is desirable to have in the system a "device" that has no physical reality. 
Such a device can have whatever peculiar characteristics are useful to resolving particular system 
design requirements. The characteristics and behavior of such a device are determined entirely by 
the driver. The driver that will be used as an example defines a pair of related nonphysical devices 
that, together, allow a large number of user tasks to coordinate access to a single system resource 
(typically, an array processor). 

5.3.1 Purpose of a Nonphysical Device Driver 

The purpose of this nonphysical device driver is to permit several tasks to share one or more devices 
in a manner not supported under the standard features of OS/32. This driver provides the ability for 
one task to do several I/O operations to a device, separated by time intervals which may be quite 
long. The driver prevents any other task sharing that device from doing any I/O operations to that 
device. The standard support in OS/32 permits a shared device to be accessed by multiple tasks on a 
first-come, first-served basis and, thus, provides no mechanism whereby one task can have exclusive 
access to the device for a prolonged period of time (and at the same time, share that device with 
other tasks). 

5.3.2 Coding a Nonphysical Device Driver 

The method implemented here was chosen over several alternatives, on the basis of central 
processing unit (CPU) overhead required to maintain the controlled access to the device. 

This nonphysical device driver does not provide any "automatic" or "guaranteed" access control to a 
device or devices. It provides proper access coordination only among "friendly" tasks, all of which 
agree to use the conventions defined by this nonphysical device. The use of this "coordination 
device" can be illustrated by the following example: assume that two devices are to be shared among 
any number of tasks, with access controlled by these nonphysical devices. Assume the devices are 
named DEVI: and DEV2:. Further, assume that these two nonphysical devices are named GET: 
and REL:. Then, each task sharing actual devices DEVI: and DEV2: need to have the following 
logical units assigned: DEVI:, DEV2:, GET: and REL:. Assume that these are (for the purposes of 
this example) LU 6 = DEVI:, LU 7 = DEV2:, LU 8 = GET: and LU 9 = REL:. To gain access to 
either DEVI: or DEV2:, the task requests access permission by issuing a read to the "device" GET:, 
such as: 



5-6 48-190 F00 R00 



READ (8, 900) NAME 
900 FORMAT (1A4) 

When either DEVI: or DEV2: is available, the read operation completes, and the fullword 'NAME' 
contains the device mnemonic of the available device (either DEVI: or DEV2:). Thus, after the 
read, 'NAME' would, in this example, contain the ASCII string "DEVI" or "DEV2", depending 
upon which device was free. 

When the task has completed its series of I/O operations to the device, the task releases the device 
to some other task by writing the name of the device to the "REL:" nonphysical device: 

WRITE (9, 900) NAME 

In this example, the contents of 'NAME' is the same ASCII string that was last read from the 
"GET:" device. It is the responsibility of the individual user tasks (u-tasks) to correlate the device 
name to the specific logical unit (lu) assignment applicable to the task in question. 

This driver utilizes a special input/output handler (IOH) entry to force special code to be executed 
upon system initialization. By having a special routine that executes only at system initialization 
time, the driver can initialize itself once, thus reducing the amount. 



**C0RD 

MLIBS 8,9,10,11 
INITCORD PROG SYSTEM COORDINATION NONPHYSICAL DEVICE 

NLIST 

$REGS$ 

$DCB$ 

$CCB 

$TCB$ 

$I0H 

LIST 

EXTRN DMT , DIRDONE , EVRTE , I ODONE , SQ 

EXTRN SV1FCER, SVC1READ, SVC1WRIT, SVC1N00P 

EXTRN COMEOT 

E NTR Y INI TCORD , TERMCORD , CORDE OT , CORD I N I T 
* 

* The following structure defines a device-dependent part of 

* the DCB. This section is used to coordinate 

* access to the limited- access devices. This is defined here 

* rather than in a separate structure macro as a matter of 

* convenience of its presentation to the reader. 
* 

DCB.DTBL STRUC 

DS DCB.CCB DEFINE DEVICE DEPENDENT AREA 
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DS 


2 


DCB . XDCD 


DS 


2 


DCB.REQD 

* 


EQU 


* 


DCB . DCBT 


DS 


4*20 


DCB.TCBT 


DS 


4*20 


DCB . DMNT 


DS 


4*20 


DCB.SIZT 


DS 


4 


DCB.PEND 


DS 
ENDS 


4 


INITCORD 


EQU 


* 



ADDR OF ASSOCIATED CCB 
DCB.DCOD OF CONTROLLED RESOURCE 
ADDRESS OF ASSOCIATED DCB243-SET UP AT 
* SYS INIT TIME. 

TABLE OF DCBS OF CONTROLLED UNITS 
TABLE OF TCBS ASSOCIATED WITH DCB'S 
TABLE OF ASSOCIATE DEVICE MNEMONICS 
POINTER/COUNTER - ENTRIES IN TABLES 
REQUEST-PENDING FLAG 



DCB 243 is a read-only device, whereas DCB 244 is a write-only device. 
A task requesting access to the control led-access device issues a read 
to the nonphysical device system generated (sysgened) as device code 243. 
When the controlled resource is available, the read goes to 
I/O completion, putting the device mnemonic of the available 
control led-access device into the calling task's I/O buffer. A task 
wishing to release a controlled resource writes to the nonphysical 
device sysgened as device code 244, with the device mnemonic of the 
device being released in the I/O buffer specified in the 
SVC1 write block. 
* 

* ON ENTRY TO THE DRIVER, DETERMINE WHICH TYPE OF NONPHYSICAL DEVICE 

* THE I/O OPERATION IS DIRECTED TOWARD. 



* FIRST, BE SURE THE TIME-OUT CONSTANT IS SET SO THAT WE 

* CAN NEVER BE TIMED OUT. 

LHI U0,X'7FFF' 



STH UO, DCB. TOUT (UD) 

LB UO, DCB.DCOD (UD) 

CHI UO, 243 

BNE INIT. 100 



GET OUR DEVICE CODE 

TEST WHICH TYPE 

DCB 244 PROCESSED ELSEWHERE, 



* THE READ-ONLY DCB WAS REFERENCED. VERIFY THIS IS A READ OPERATION 

* AND IF NOT, RETURN AN ILLEGAL FUNCTION STATUS. 



LB UO,DCB.FC(UD) 

NHI U0,X'60' 

CHI U0,X'40' 

BNE INIT. 200 



GET THE CALLER'S FUNCTION 
SAVE ONLY FUNCTION BITS 
CHECK FOR READ 
IF NOT, ERROR OUT 



* NOW TEST THE I/O AREA TO BE SURE THERE IS ENOUGH AREA 
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L UO,DCB.EADR(UD) 

S UO,DCB.SADR(UD) 

CHI U0,3 

BM INIT.210 



PARITY ERROR IF NOT ENUF ROOM 



* NOW LOOK FOR A FREE RESOURCE. 

L U1,DCB.SIZT(UD) 

INIT.OIO SIS Ul>4 

BM INIT.050 

L UO,DCB.TCBT(UD,Ul) 



BNZ 



INIT.OIO 



GET SIZE OF TABLE 

DECREMENT POINTER 

IF NOTHING AVAILABLE, WAIT 

TEST AN ENTRY FOR AVAILABILITY 

IF NOT AVAILABLE, TRY NEXT ONE 



* A CONTROLLED RESOURCE IS AVAILABLE, SO ASSIGN THE RESOURCE 

* TO THIS TASK, GIVE THE TASK THE DEVICE MNEMONIC OF THE RESOURCE, 

* AND EXIT 



INIT.020 L 


UO,DCB.DMNT(Ul,UD) 


L 


U2 , DCB . SADR (UD) 


EXHR 


UO,UO 


STH 


UO,0(U2) 


EXHR 


UO,UO 


STH 


UO,2(U2) 


LIS 


U0,4 


ST 


UO,DCB.LLXF(UD) 


LIS 


UO,0 


STH 


UO, DCB. STAT (UD) 


ST 


UO,DCB.PEND(UD) 


L 


UO,DCB.TCB(UD) 


ST 


UO,DCB.TCBT(Ul,UD) 


B 


IODONE 



GET NAME OF AVAILABLE DEVICE 

GET THE START ADDRESS OF THE BUFFER 

AND PUT THE DEVICE MNEMONIC OUT 

* 
* 

SET LENGTH OF XFER 
* 

SET STATUS = O 
* 

CLEAR THE REQUEST-PENDING FLAG 
GET REQUESTING TCB ID 
AND SAVE TO SHOW IN USE 
ALL DONE. 



* COME HERE IF THERE IS NO CONTROLLED RESOURCE AVAILABLE 

* WHEN A REQUEST IS ISSUED. SET A FLAG TO INDICATE THAT 

* A REQUEST IS PENDING, AND THEN EXIT TO DIRDONE . 



INIT.050 LIS UO,l 

ST UO,DCB.PEND(UD) 
B DIRDONE 



SET REQUEST PENDING FLAG 
AND EXIT 



* PROCESS AN I/O DIRECTED AT A DCB 244 DEVICE. VERIFY THE 

* REQUEST IS A WRITE. IF IT IS NOT, EXIT WITH AN ILLEGAL 
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* FUNCTION ERROR. IF IT IS A WRITE , VERIFY THERE ARE AT LEAST 

* FOUR BYTES IN THE I/O BUFFER. IF NOT, EXIT WITH A PARITY 

* ERROR CODE. IF AT LEAST 4 BYTES EXIST, USE THE FIRST FOUR 

* BYTES AS A DEVICE MNEMONIC. SCAN THE INTERNAL TABLE FOR THE 

* CONTROLLED DEVICE, AND, IF FOUND, VERIFY THAT THE 

* CALLING TCB IS THE SAME AS THE TCB ID IN THE TABLE. 

* IF IT IS NOT, EXIT WITH A DEVICE UNAVAILABLE ERROR. IF THE 

* TCB IS THE SAME, CLEAR THE TCB ENTRY IN THE TABLE. 

* IF THE TCB DOES NOT MATCH, EXIT WITH AN UNRECOVERABLE ERROR. 

* THEN CHECK FOR ANY REQUEST OUTSTANDING. IF SO, SCHEDULE AN 

* EVENT AGAINST THE READ DEVICE. THEN EXIT. 



INIT.IOO LB 


UO,DCB.FC(UD) 


NHI 


UO,X"60' 


CHI 


UO,X'20' 


BNE 
■it 


INIT.200 


L 


UO,DCB.EADR(UD) 


S 


UO,DCB.SADR(UD) 


CHI 


UO,3 


BM 


INIT.210 


L 


U2,DCB.SADR(UD) 


LH 


UO,0(U2) 


SLL 


U0,16 


OH 


UO,2(U2) 


L 


UCDCB.REQD(UD) 


L 


U1,DCB.SIZT(UC) 


INIT.llO SIS 


Ul,4 


BM 


INIT.220 


C 


UO , DCB . DMNT (Ul , UC) 


BNE 

•if 


INIT.llO 


L 


UO,DCB.TCB(UD) 


C 


UO,DCB.TCBT(Ul,UC) 


BNE 


INIT.230 


LIS 


UO,0 


ST 
* 


UO,DCB.TCBT(Ul,UC) 


L 


UO,DCB.PEND(UC) 


BZ 


IODONE 


L 


UO, DCB. LEAF (UC) 


ATL 


UO,SQ 


BZ 


IODONE 



GET THE CALLER'S FUNCTION CODE 
MASK ALL BUT FUNCTION BITS 
IS IT A WRITE? 
IF NOT, ILLEGAL FUNCTION. 

CHECK THE BUFFER LENGTH 



IF NOT, IT IS A PARITY ERROR. 
GET THE BUFFER ADDRESS AGAIN. 
GET THE CONTENTS OF THE BUFFER 



GET ADDRESS OF REQUEST DCB 

GET THE SIZE OF THE INTERNAL TABLE 

DECREMENT THE POINTER 

IF NOT FOUND, GIVE BACK D-U 

IS IT THIS ENTRY? 

NO, TRY NEXT ENTRY. 

GET TCB OF REQUESTER. 

AND CHECK AGAINST TABLE. 

IF WRONG TASK, GIVE UNRECV ERR 

ALL IS O.K., SO RESET TABLE 



GET THE REQUEST-PENDING FLAG 

IF NONE, ALL DONE 

IF REQ. PENDING, SCHEDULE ESR. 

* 

AND THEN WE ARE DONE. 
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* ERROR EXITS 

* 

I NIT. 200 LHI 

B 
INIT.210 LHI 

B 
INIT.220 LHI 

B 
INIT.230 LHI 

B 



U0,X'C000' 

INIT.250 

U0,X'8282* 

INIT.250 

UCX'AOOO' 

INIT.250 

U0,X'8400' 

INIT.250 



ILLEGAL FUNCTION 



PARITY ERROR - I/O BUFFER TOO SMALL 



D-U IF NO SUCH DEVICE 



UNRECV IF WRONG TASK TRYING RELEASE 



* ON ERROR EXIT, PUT ERROR CODE IN DCB AND EXIT 
* 



INIT.250 STH UO, DCB. STAT (UD) 
B IODONE 



* TERMINATION (ESR) ENTRY POINT. 
TERMCORD EQU * 

* 

* THIS ROUTINE WILL BE ENTERED ONLY IF A REQUEST HAS BEEN PENDING, 

* AND THERE IS NOW A FAIR CHANCE THAT A CONTROLLED RESOURCE IS NOW 

* AVAILABLE. IF A REQUEST GETS THIS FAR, THE I/O BUFFER HAS BEEN 

* CHECKED FOR CORRECT SIZE, SO ALL THAT IS NEEDED IS TO LOCATE 

* THE FREE RESOURCE, INFORM THE CALLING TASK, MARK THE RESOURCE AS 

* IN USE, AND EXIT TO IODONE. 
* 

* THE FOLLOWING LOOP SCANS THE INTERNAL TABLE FOR A FREE RESOURCE. 



TERM. 010 SIS 
BM 

L 



U1,DCB.SIZT(UD) 

Ul,4 

EVRTE 

UO , DCB . TCBT (Ul , UD) 



BNZ TERM. 010 



GET SIZE OF TABLE 

DECR THE POINTER 

NOTHING FREE, SO GET OUT 

TEST AN ENTRY FOR AVAILABILITY 

NOT FREE, TRY ANOTHER ONE. 



* FOUND A FREE ENTRY. WE CAN NOW USE THE SAME PROCESSING AS THE 

* ' INIT' PHASE, GO THERE TO FINISH UP 

B INIT. 020 

* ENTRY TO CORDEOT IS VIA AN I OH ENTRY. 
* 

* THIS ROUTINE IS ENTERED VIA A BALR U8,U8 FROM EXSV. SETTING 

* IOH.EOT FORCES BYPASSING THE COMEOT HANDLER (DEFAULT SET BY 

* EXSV) . UPON RETURN TO EXSV, REGISTER NINE IS RELOADED WITH 
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* THE TCB ADDRESS BUT NO OTHER REGISTERS ARE PRESERVED BY THE 

* CALLING ROUTINE. 
* 

* REFER TO MODULE EXSV FOR ADDITIONAL DETAILS 

CORDEOT EQU * 
* 

* UPON ENTRY U9 = TCB ADDR OF TASK GOING TO EOT 

* UA = DCB ADDR OF THE DEVICE FOR WHICH EOT PROCESSING 

* -IS NOW BEING PERFORMED. 
* 

* EOT PROCESSING WILL CONSIST OF ZEROING OUT THE TCB TABLE ENTRY 

* FOR ANY DEVICE WHICH HAS THIS TCB ADDRESS IN ITS 'DCB.TCBT' 

* FIELD IN THE INTERNAL CONTROL TABLES. THEN, CHECK FOR ANY 

* REQUEST OUTSTANDING - IF SO, PROCESS THE REQUEST. 
* 

L UD,DCB.REQD(UA) GET ADDRESS OF DCB FOR 
LR UF,UA SAVE DCB ADDRESS 

* ACQUISITION SIDE. 

L UA,DCB.SIZT(UD) GET SIZE OF CONTROL TABLE. 

EOT. 01 SIS UA,4 DECREMENT THE POINTER 

BM EOT. 03 IF NOTHING ELSE, WE ARE DONE 

C U9,DCB.TCBT(UA,UD) IS THIS AN ENTRY TO BE RESET? 

BNE EOT. 02 

LIS UC,0 GET A ZERO 

ST UC, DCB.TCBT (UA,UD) CLEAR THE ENTRY. 

EOT. 02 LR UA,UA ARE WE AT END OF TABLE 

BP EOT. 01 GO UNTIL DONE 
* 

* IT IS NOW NECESSARY TO CHECK FOR ANY UNHONORED REQUESTS PENDING. 
* 

L UCDCB.PEND(UD) TEST THE REQUEST PENDING FLAG 

BZ EOT. 03 IF NO REQUEST, WE ARE ALL DONE 

C U9,DCB.TCB(UD) IS REQUESTER THIS TASK? 

BZ EOT. 03 IF SO, DO NOTHING 

L UC, DCB. LEAF (UD) OTHERWISE, SCHEDULE AN EVENT 

ATL UC,SQ ON THIS DCB 

EOT. 03 EQU * 

LR UA,UF RESTORE FOR COMEOT 

B COMEOT * GO TO STANDARD EOT HANDLING 

* INIT ROUTINE WHICH IS EXECUTED DURING SYSINIT. 

* THE SYSINIT ROUTINE SAVES REGISTERS EIGHT THROUGH 
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* FIFTEEN BEFORE IT BRANCHES TO THE I OH ENTRY. 

* THE BRANCH IS PERFORMED BY A BALR E8,ED. 

* ED--HAS BEEN LOADED WITH THE IOH INIT ENTRY--IF THIS 

* ENTRY IS ZERO--SYSINIT DOES NOTHING WITH IT. 



* 



THUS THE IOH. INIT ROUTINE MAY USE REGISTERS 9 THROUGH 



* FIFTEEN TO GET ITS JOB DONE. 
* 

* THE BRANCH REGISTER TO RETURN FROM AN IOH ENTRY IS REGISTER EIGHT 
* 

* UPON ENTRY TO THE IOH ROUTINE UB = DCB ADDRESS 

* 

* REFER TO MODULE EXIN FOR ADDITIONAL DETAILS 
* 

CORDINIT EQU * 
* 

* THERE ARE TWO SEPARATE TYPES OF SYSTEM INITIALIZATION, ONE FOR 

* THE ACQUISITION NON-PHYSICAL DEVICE, AND ONE FOR THE RELEASE 

* NON-PHYSICAL DEVICE. BRANCH TO THE APPROPRIATE ROUTINE BASED ON THE 

* DEVICE CODE OF THE NON-PHYSICAL DEVICE. 
* 

* ON ENTRY, UB = A (DCB) OF COORDINATION NONPHYSICAL DEVICE 
* 

LB UE,DCB.DCOD(UB) GET DEVICE CODE 

CHI UE,243 

BE INIT. 00 

BNE INIT. 10 
* 

* GO THRU THE DEVICE MNEMONIC TABLE AND BUILD A LIST OF 

* DCB ADDRESSES CORRESPONDING TO ALL THE DEVICES USING THE 

* DEVICE CODE SPECIFIED IN 'DCB.XDCD' 
* 

INIT. 00 LH UE,DCB.XDCD(UB) GET DEVICE CODE WE ARE TO CONTROL 

LIS UA,0 COUNTER, AND POINTER TO INTERNAL TABLE 

LA UF,DMT GET ADDRESS OF DMT 

INIT. 01 AIS UF,8 INCREMENT POINTER TO DEVICE MNEMONIC TABLE 

L UC,4(UF) GET A DCB ADDRESS 

BZR U8 IF END OF TABLE, WE ARE DONE 

LB UD,DCB.DCOD(UC) GET THE DEVICE CODE OF THIS DEVICE 

CR UD,UE IS THIS ONE WE ARE INTERESTED IN? 

BNE INIT. 01 IF NOT, GO GET NEXT ENTRY 

ST UC,DCB.DCBT(UA,UB) SAVE THIS DCB 

LIS UC,0 GET A ZERO 
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ST UC,DCB.TCBT(UA,UB) ZERO THE TCB ENTRY FOR THIS DCB. 

L UD,0(UF) GET THE DEVICE MNEMONIC FOR THIS DEVICE 

ST UD,DCB.DMNT(UA,UB) AND SAVE IT IN THE TABLE 

AIS UA, 4 INCREMENT THE POINTER TO NEXT SLOT 

ST UA,DCB.SIZT(UB) SAVE THE POINTER 

B I NIT. 01 AND GO GET NEXT ENTRY 
* 

* GO THROUGH THE DEVICE MNEMONIC TABLE AND FIND THE DCB FOR 

* THE ACQUISITION NONPHYSICAL DEVICE WHICH IS SYSGENED TO CONTROL 

* THE SAME DEVICE CODE AS THE DCB FOR WHICH THIS ENTRY WAS MADE. 

* PUT THE ADDRESS OF THAT DCB INTO THE RESERVED SPACE IN THE 

* DCB FOR WHICH THIS PROCESSING IS BEING PERFORMED. 
* 

GET DEVICE CODE WE ARE TO CONTROL 

GET ADDRESS OF DEVICE MNEMONIC TABLE 

INCREMENT POINTER TO DEVICE MNEMONIC TABLE 

GET A DCB ADDRESS 

IF END OF TABLE, WE ARE DONE 

GET THE DEVICE CODE OF THIS DEVICE 

IS THIS AN ACQUISITION NONPHYSICAL DEVICE 

DOES IT CONTROL THE SAME DCOD WE DO? 
IS THIS ONE WE ARE INTERESTED IN? 
IF NOT, GO GET NEXT ENTRY 
SAVE THIS DCB ADDRESS 
ALL DONE 
* 

* DEFINE THE IOH LIST FOR ACQUISITION DEVICE 
* 

I OH NAME=CRD1 . I OH , 1 

READ=SVC1READ, 1 

WRITE=SVC1N00P, 1 

WAIT=SVC1N00P, 1 

HALT=SVC1N00P, 1 

EOT=0, 1 

TEST=SVC1N00P, 1 

SET=SVC1N00P , 1 

REW=SVC1N00P, 1 

BSR=SVC1N00P, 1 

FSR=SVC1N00P, 1 

WFM=SVC1N00P, 1 

FFM=SVC1N00P , 1 

BFM=SVC1N00P , 1 
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INIT.IO 


LH 


UE,DCB.XDCD(UB) 




LA 


UF,DMT 


INIT.ll 


AIS 


UF,8 




L 


UC,4(UF) 




BZR 


U8 




LB 


UD, DCB. DCOD (UC) 




CHI 


UD, 243 




BNE 


INIT.ll 




LH 


UD,DCB.XDCD(UC) 




CR 


UD,UE 




BNE 


INIT.Ol 




ST 


UCDCB.REQD(UB) 




BR 


U8 



INIT=CORDINIT 

* DEFINE THE IOH LIST FOR RELEASE DEVICE 
* 

IOH NAME=CRD2.IOH, 1 

READ=SVClNOOP / 1 

WRITE=SVC1WRIT, 1 

WAIT=SVClNOOP, 1 

HALT=SVClNOOP / 1 

EOT=CORDEOT, 1 

TEST=SVClNOOP, 1 

SET=SVClNOOP, 1 

REW=SVClNOOP , 1 

BSR=SVClNOOP , 1 

FSR=SVClNOOP, 1 

WFM=SVClNOOP , 1 

FFM=SVClNOOP, 1 

BFM=SVClNOOP , 1 
INIT=CORDINIT 

END 

BEND 

SYSGEN32 DCB macros for nonphysical device driver: 

MACRO 

DCB243 %DCOD= , %DN= , %CLAS= , %I LVL= , %NAME= , %SHCCB= , 1 

%SLCH=,%XDCD= 
GBLB %DCB$ , %PDCB, %DDCB, %EVN, %CCB, %DFLG, %SDCB 
GBLB %IDCB, %ODCB, %S125DCB, %ICCB, %BDCB 
GBLB %ADCB , %TCB , %I OB , %I 0B$ , %CRTDCB , %LPDCB 
GBLB %MMDDX , %DDEX , %VFDCB , %MTP , %CRPDCB , %MGDCBX , %HFWDST 
GBLB %PSDCBX , %CRDP , %AOBDCB , %BI OCDCB , %LPTDCB 
GBLB %C0RD243 
GBLC %IDVAL 
BGBLA %ID243 
LCLA %CCBFL 
LCLA %CLASN 
LCLC %RXLT,%RQU 
LCLC %CORDNM,%PTRPAS 
LCLC %OFFS 
LCLA %RDN 

LCLC %MDN , %MCNT , %MSLCH 
LCLA %TRCNT,%UPTR 



48-190 F00 R00 5.15 



%RQU 

%MDN SETC 
%CCBFL SETA 
%C0RD243 SETB 

AIF 
%CLASN 
&CLSNTD 



LCLB %FOUND,%DA 
BGBLA %FIRST 
SETC * COMQ ' 

'%DN' 





(T'%CLAS EQ 'U'J&CLSNTD 

%CLAS*12 IOCLASS*12 



DEFAULT DEVICE QHANDLER 
DEVICE ADDRESS 



CONVERT CURRENT ID TO HEX. 



CCBI 
CCB%NAME EQU 
%ID243 SETA 
&DCBOPT ANOP 
DCB%DCOD%IDVAL 
%OFFS SETC 
DCB.%NAME EQU 



SETA 

ANOP 

CONVNUM VAL=%ID243 

USERINIT 

$DCB$ 

DCBI DCOD=243, SIZE=DCB.DVDP+4, INIT=INITCORD, 

TERM=TERMCORD , FLGS=DFLG . LNM+DFLG . UCM. 

ID=%IDVAL, ATRB=EB80, C0PY=$C0RD243 , IOH=CRDl . IOH 

DCOD=243, ID=%IDVAL, SUBA=III 

CCB%DCOD%IDVAL 



1 
2 



%ID243+1 



PROG USER DCB 

'%DCOD' : '%IDVAL' 

DCB%OFFS 
ENTRY DCB.%NAME 
ORG DCB%OFFS+DCB.DMT 
DC DMT . %NAME 
EXTRN DMT.%NAME 
ORG DCB%OFFS+DCB.DN 

H'%DN' 

DCB%OFFS+DCB.LEAF 



ESTABLISH PROPER OFFSET 



DEVICE ADDRESS 



DC 
ORG 
AIF 
DAC 



&NSLEAF 



&NRMLFX 


ANOP 


&NOLEAF 


ANOP 




AIF 




ORG 




DC 


&NOCLAS 


ANOP 



LEAF POINTER 
(T'JSSHCCB 1 EQ 'U')&NSLEAF B IF NOT SHARED 
LF%SHCCB USE SHARED DEVICE LEAF 

EXTRN LF%SHCCB 
AGO &NRMLFX 
ANOP 

DAC LF%OFFS GENERATE STANDARD LEAF NAME 

EXTRN LF%OFFS 



(T'%CLAS EQ 'U')&NOCLAS 
DCB%OFFS+DCB.CLAS 10 CLASS 
H'%CLASN' I0CLASS*12 
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&NOILVL 



&NOQU 



%RDN 



(T*%ILVL EQ 'U'J&NOILVL 
DCB%OFFS+DCB.ILVL ILEVEL 
H'%ILVL' 

('JCRQU* EQ ")&NOOU 
DCB%OFFS+DCB.Q 
%RQU 
%RQU 



DGB%OFFS+DCB . XDCD 

%XDCD 

DCB%OFFS+DCB.SIZT 

O 

DCB%OFFS+DCB.PEND 



$ST%OFFS 



AIF 
ORG 
DC 
ANOP 
AIF 
ORG 
DAC 
EXTRN 
ANOP 
ORG 
DC 
ORG 
DC 
ORG 
DC 
ORG 
ASIS 
END 
SETA 
MEND 
MACRO 

DCB244 %DCOD=, %DN=, %CLAS=, %ILVL=, %NAME=, %SHCCB=, 
%SLCH=,%XDCD= 

%DCB$ , %PDCB, %DDCB, %EVN, %CCB, %DFLG, %SDCB 

%IDCB, %ODCB, %S125DCB, %ICCB, %BDCB 

%ADCB , %TCB , %I OB . %I OB$ , %CRTDCB , %LPDCB. 

%MMDDX , %DDEX , %VFDCB , %MTP , %CRPDCB , %MGDCBX , %HFWDST 

%PSDCBX, %CRDP , %AOBDCB, %BIOCDCB, %LPTDCB 

%C0RD244 

%IDVAL 



ORG TO END OF DCB 



%DN+1 



GBLB 
GBLB 
GBLB 
GBLB 
GBLB 
GBLB 
GBLC 



BGBLA %ID244 
LCLA %CCBFL 
LCLA %CLASN 
LCLC %RXLT,%RQU 
LCLC %CORDNM,%PTRPAS 
LCLC %OFFS 
LCLA %RDN 

LCLC %MDN , %MCNT , %MSLCH 
LCLA %TRCNT,%UPTR 
LCLB %FOUND,%DA 
BGBLA %FIRST 
%RQU SETC * COMQ ' 



DEFAULT DEVICE QHANDLER 
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%MDN 


SETC 


1 1 


%CCBFL 


SETA 





%C0RD244 


SETB 
AIF 



(' 


%CLASN 


SETA 


% 


&CLSNTD 


ANOP 





%DN' 



DEVICE ADDRESS 



CCBI 
CCB%NAME EQU 
%ID244 SETA 
&DCBOPT ANOP 
DCB%DCOD%IDVAL 
%OFFS SETC 
DCB.%NAME EQU 



(T'%CLAS EQ 'U')&CLSNTD 
%CLAS*12 IOCLASS*12 



CONVNUM VAL=%ID244 CONVERT CURRENT ID TO HEX. 

USERINIT 

$DCB$ 

DCBI DCOD-244, SIZE=DCB.DVDP+4, INIT=INITCORD, 

TERM=TERMCORD, FLGS=DFLG . LNM+DFLG . UCM, 

ID=%IDVAL, ATRB=EB80 / COP Y=$ CORD 2 44, IOH=CRD2 . IOH 

DC0D=244, ID=%IDVAL / SUBA=III 

CCB%DCOD%IDVAL 



1 
2 



%ID244+1 



PROG USER DCB 

^DCOD' : '%IDVAL' 

DCB%OFFS 
ENTRY DCB.%NAME 
ORG DCB%OFF S +DCB . DMT 
DC DMT.%NAME 
EXTRN DMT.%NAME 
ORG DCB%OFFS+DCB.DN 

H*%DN' 

DCB%OFFS+DCB . LEAF 



ESTABLISH PROPER OFFSET 



DEVICE ADDRESS 



DC 
ORG 
AIF 
DAC 



&NSLEAF 



&NRMLFX 
&NOLEAF 



&NOCLAS 



&NOILVL 



LEAF POINTER 
(T'%SHCCB' EQ 'U'J&NSLEAF B IF NOT SHARED 
LF%SHCCB USE SHARED DEVICE LEAF 

EXTRN LF%SHCCB 
AGO &NRMLFX 
ANOP 

DAC LF%OFFS GENERATE STANDARD LEAF NAME 

EXTRN LF%OFFS 
ANOP 
ANOP 
AIF 
ORG 
DC 
ANOP 
AIF 
ORG 
DC 
ANOP 



(T'%CLAS EQ 'U')&NOCLAS 
DCB%OFFS+DCB.CLAS 10 CLASS 
H'%CLASN' I0CLASS*12 

(T*%ILVL EQ 'U')&NOILVL 
DCB%OFFS+DCB.ILVL ILEVEL 
H'%ILVL' 
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&NOQU 



%RDN 



AIF 


( ' %RQU ' EQ ' * ) &NOQU 


ORG 


DCB%OFFS+DCB.Q 


DAC 


%RQU 


EXTRN 
anop 


%RQU 


ORG 


DCB%OFFS+DCB . XDCD 


DC 


%XDCD 


ORG 


DCB%OFFS+DCB.REQD 


DC 





ORG 


$ST%OFFS 


ASIS 




END 




SETA 


%DN+1 


MEND 





ORG TO END OF DCB 



Macros used for COPY in DCBI macro for nonphysical device driver: 

MACRO 

$C0RD243 

GBLB %C0RD243 

AIF (NOT %C0RD243) &NEEDIT 

MEXIT 

> 1 

TABLE OF ASSOCIATED STRUCTURES FOR COORDINATION 
DEFINE DEVICE -DEPENDENT AREA 



TABLE OF DCBS ON CONTROLLED UNITS 
TABLE OF TCBS ASSOCIATED WITH DCBS 
TABLE OF ASSOCIATED DEVICE MNEMONICS 
POINTER/COUNTER - ENTRIES IN TABLE 
REQUEST-PENDING FLAG 



&NEEDIT 


ANOP 




%CORD243 


SETB 1 


CORD243 


STRUC 




DS 


DCB.i 




DS 


2 


DCB. XDCD 


DS 


2 




ALIGN 


4 


DCB.DCBT 


DS 


4*20 


DCB.TCBT 


DS 


4*20 


DCB.DMNT 


DS 


4*20 


DCB.SIZT 


DS 


4 


DCB.PEND 


DS 

ENDS 

MEND 


4 



MACRO 

$C0RD244 

GBLB %C0RD244 

AIF (NOT %C0RD244) &NEEDIT 

MEXIT 
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&NEEDIT 


ANOP 


%C0RD244 


SETB 1 


C0RD244 


STRUC 




DS DCB.CCB 




DS 2 


DCB.XDCD 


DS 2 




ALIGN 4 


DCB.REQD 
* 


DS 4 




ENDS 




MEND 



TABLE OF ASSOCIATED STRUCTURES FOR COORDINATION 
BASIC DCB SIZE 



ADDRESS-OF ASSOCIATED DCB243-SET UP 
* AT SYS-INIT TIME. 



5.4 SUPERVISOR CALL 6 (SVC6) AND TRAP GENERATING DEVICE DRIVERS 

In certain system configurations, it is desirable to have an external device cause a certain piece of 
user's task code to be executed in response to a signal from that device. An example of such a 
situation is the existence of an external clock signal, which can be used to synchronize a cyclical 
processing activity, such as is found in flight simulators and process control systems. 

5.4.1 Function of a Trap Generating Device Driver 

In the case of the external synchronization signal (or clock pulse), no data is being transferred to or 
from the device. Rather, we simply want to have some particular set of user-level code that is to be 
executed in response to that external signal. The appropriate interface between the user-level 
program and the clocking signal is a trap generating device driver, using the SVC6 interface for 
such devices. To use this feature, the user's task must be set up to handle task traps and process 
items on a task queue. The user's task then "connects" itself to this trap generating device (i.e., 
clock pulse), and "thaws" (enables) the interrupts from the device by issuing an SVC6 instruction. 
The driver then adds items to the task's queue each time an interrupt occurs, which causes the task 
to be forced by the operating system to execute a prespecified piece of code. In this way, the 
external hardware signal can cause a specific section of user-level code to be executed each time an 
interrupt occurs. 

5.4.2 Coding a Trap Generating Device Driver 

The system designer should note that a trap generating device cannot also be defined (through the 
DCB) as a "normal" SVC1 interface device. However, a normal SVC1 device driver can be used to 
add items to a user's task queue (and thus cause task traps) in response to specific situations. 
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MLIBS 8,9,10 

$REGS$ 

$DCB$ 

$CCB 

$TCB$ 

EXTRN EVRTE,III,ISPTAB,SQ,TMATQ1 

ENTRY CMDTGD, INITTGD, ISRTGD, TERMTGD 



* The function processing part of this driver is entered from 

* the SVC6 processor in the operating system via the following 



* instructions: 
* 



L UB / DCB.FUNC(UD) 
BALR UE,UB 



* On entry from the SVC6 processor, the following register 

* conventions apply: 
* 

* RD = address of the DCB of the trap generating device 

* RE = address in SVC6 processor to return to after 

* performing the requested function. 



* 
* 
* 
* 
* 
* 
* 
* 
* 

INITTGD 
* 

CMDTGD 

* 

* 



Note that DCB. EC has been set up by the SVC6 processor 
to be one of the following values: 



DCB. EC = X'CO* 
DCB.FC = X'AO' 
DCB.FC = X*90' 



for "thaw" function 

for " freeze" function 

for "simulate interrupt" function 



(these are the only three values that can appear) 
EQU * 



EQU 



LH 
LB 
LHL 



not used - needed to satisfy 
DCB.INIT reference only. 

entry point specified in the 
DCB.FUNC term of the DCB. 



U2,DCB.DN(UD) 
U3,DCB.FC(UD) 
UCDCB.CCB(UD) 



get the device address 
get the function code 
get CCB address 



CHI 
BE 



U3,X'C0' 
TGDTHAW 



"thaw" function? 
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CHI U3,X'A0' 

BE TGDFREZ 

CHI U3,x'90' 

BE TGDSINT 



"freeze" function? 



"simulate interrupt" function? 



* We should NEVER "fall through" all three tests. Thus, to 

* assist in debugging an "impossible" situation, we will simply 

* put a halt instruction here, so that if the "impossible" ever 

* happens, we can easily examine all of the relevant registers 

* and locations to see how we got here. 
* 

HALT should never be executed. 

* 

* Process "thaw" function: set up the interrupt path to the 

* interrupt service routine, and enable the interrupt hardware 

* on the device. 



TGDTHAW EQU 


* 


LA 


UCISRTGD 


STH 


UO,CCB.SUBA(UC) 


LIS 


U0,0 


STH 


UO,CCB.CCW(UC) 


AIS 


UC,1 


STH 


UC,ISPTAB(U2,U2) 



get the address of the ISR 

& put into the CCB. 

get a zero, 

& reset the channel command word 

make the CCB address odd 

& set up the ISP table 



commands to enable hardware interrupts on the device go here 
BR UE return to the SVC6 processor 



* Process "freeze" function: dismantle the interrupt path to the 

* interrupt service routine, and disable the interrupt hardware 

* on the device . 



TGDFREZ 



EQU 

LA 

STH 



UO,III 
UO,ISPTAB(U2,U2) 



get the address of the null 
interrupt routine & res€9t the ISPT 
(note that since we do this, there 
is no reason to also reset the 
CCB.SUBA value) 



* commands to disable hardware interrupts on the device go here. 



BR 



UE 



return to the SVC6 processor 
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* Process "slnt" function: simulate an interrupt on the device. 

* Note: interrupts from the device, either real or simulated, 

* can not be taken until the "thaw" function has been executed. 

* 



TGDSINT EQU * 

LH U7,DCB.ILVL(UD) 

SINT U7,0(U2) 

BR UE • ■ 



get the proper interrupt level 
generate the "interrupt" 
return to SVC6 processor 



Interrupt service routine: when an interrupt from the device 
is received, schedule the Event Service Routine (ESR) for 
execution. Typically, a trap generating device needs no further 
commands from the processor once interrupts are enabled. Thus, 
it is unlikely that the ISR will contain any hardware Interface 
command instructions. 



PURE 
ISRTGD EQU * 

L E5,CCB.DCB(E4) 
L E6,DCB.LEAF(E5) 
ATL E6,SQ 
LPSWR EO 



get the address of the DCB 
get the item to be put on 
the system queue, and add it 
exit the ISR. 



* Event Service Routine: The ESR adds an item to the. user's 

* task queue, by calling a routine in the operating system. 





IMPUR 




TERMTGD 


EQU 


* 




L 


U9,DCB.TCB(UD) 




L 


UA,DCB.PBLK(UD) 


* 






* 








NI 


UA,Y , FFFFFF , 


* 






* 






* 








BAL 


U8,TMATQ1 


* 






* 








B 


EVRTE 




END 





get the user ' s TCB address 
get the task queue parameter 
that was specified by the 
user in the "connect" function 
& be sure it is 24 bits long 
(this sets the "reason code" 
as defined for task queue 
entries to be equal zero) . 
then call the OS routine 
to add this to the task's 
queue . 
Exit from the ESR. 
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APPENDIX A 



REVIEW OF ASSEMBLY LANGUAGE 



INPUT/OUTPUT (I/O) COMMANDS 



Here are some notes on the usage of Common Assembly Language/32 (CAL/32). 

When dealing with device interfaces, it is common to use I/O instructions that are rarely used under 
any other circumstances. A review of some of these commands is included here. 

Remember that all I/O commands are privileged commands. 
SENSE STATUS 



SS Rl , STAT1 



Put status into R2 of the device whose 
address is in Rl. 



SSR R1,R2 



Put status into R2 of the device whose 
address is in Rl. 



SIMULATE INTERRUPT 

SINT R1,0(R2) 



Where Rl is the interrupt level and 
R2 is the device address. 



OUTPUT COMMAND 

OC Rl, DISARM 



Disarm the interface 



DISARM DB X'CO* 



Disarm the command 



WRITE DATA/WRITE HALFWORD 

WH Rl . DCB . SADR (UD) 



Where Rl contains the device address 
and DCB. SADR (UD) is the address that 
contains the data to be written. 



NOTE 

None of the I/O commands is provided in immediate 
format! 
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APPENDIX B 
DEBUG TECHNIQUES 

This appendix is a brief discussion of two convenient debug techniques. 

• The single step method: 

This method is useful in tracing the basic flow of the driver. The systems integrator places the 
machine into single step mode (by depressing the single button on the front panel or in the case 
of a Model 3210, by using the less than (<) symbol), and then proceeds to step through the 
code. 

The single step method is not suitable for tracing any problems that are timing related. 

• Inserting 'HALT' instructions: 

A HALT (8800) instruction can be inserted into the driver code at any point. The driver is then 
free running until the HALT (breakpoint) instruction is executed. This method is often used to 
trap a driver if it is executing code that should never be reached. Some timing problems can be 
traced by way of this method. 
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APPENDIX C 
CRASH CODE ANALYSIS 

The following is a listing of crash code messages and their meaning: 

153 A crash code of 153 denotes an invalid memory alignment condition. When this occurs 

within the driver code, it is most commonly found to be a fullword reference on a 
halfword boundary. This crash may also occur if a device leaf is added to the system 
queue more than once. 

— 102 This crash code is an illegal instruction that is executed within system code. This is the 

most difficult crash to trace simply because the pointer that you have points you to the 
illegal instruction and not to the mechanism that brought you to the illegal instruction. 
The common causes are random branches (i.e., branches using the wrong register), 
and data constants not properly placed in memory. 

— 142 This crash code is caused by a supervisor call 1 (SVC1) ending parameter block 

address that is less than the SVC1 starting parameter block address. 

— -132 This crash code is caused by an illegal SVC call being issued by the driver (such as an 

SVC2 call). 
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PREFACE 



This document serves as a reference manual to the system programmer that plans to write an OS/32 
device driver to interface a nonstandard input/output (I/O) device with OS/32. This manual covers 
only device drivers accessed by the supervisor call 1 (SVC1) I/O protocol. SVC15 access is 
supported by Integrated Telecommunications Access Method (ITAM) line drivers, is not covered in 
this manual. 

This manual is divided into two parts; whereas Part I is a tutorial and Part II contains important 
background information on I/O subsystems. Chapter 1 is a discussion of the general philosophy of 
OS/32 drivers; i.e, the purpose of a driver and also contains a general outline of the required 
information and interfaces which one must understand in order to write a driver. Chapters 2 
through 5 present a detailed discussion of those interfaces which are defined by Perkin-Elmer. 
Specifically, Chapter 2 describes the Perkin-Elmer Series 3200 Processor I/O architecture. Chapter 
3 discusses various methods of I/O programming, giving sample code sequences for each. Chapter 4 
describes the OS/32 I/O subsystem architecture. This chapter is based on the I/O subsystem as of the 
OS/32 R08.1 software release, but it is generally compatible with any revision of OS/32 since 
software release R06.2. Chapter 5 is a detailed discussion of the structure of an OS/32 driver. 
Sample code sequences for the various major components are given. Chapter 6 describes the steps 
that are necessary to create a custom driver and to include it into an OS/32 system, respectively. 
Chapter 7 describes the changes that have to be implemented in drivers being written for systems 
configured under an input/output processor (IOP), as opposed to drivers that are written solely for 
systems configured under the central processing unit (CPU). Appendix A describes all the 
parameters for data structures, such as the device control block (DCB) and the channel control 
block (CCB). A detailed description of machine states is given in Appendix B. Appendix C defines 
the OS/32 macros that are used by drivers and Appendix D defines the OS/32 driver routines. 
Appendix E shows a sample driver, with its corresponding DCB macro. 

For information on the contents of all Perkin-Elmer 32-bit manuals, see the 32-Bit Systems User 
Documentation Summary. 
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CHAPTER 1 
INTRODUCTION 



1.1 INTRODUCTION 

This chapter introduces OS/32 device drivers. After discussing the general philosophy behind 
writing a driver; i.e., the purpose of a driver, an introduction to hardware and software architecture 
is provided. 

1.2 PURPOSE OF A DRIVER 

A device driver in an operating system acts as the control point for the unique physical or device- 
dependent characteristics of a peripheral device. The driver is responsible for converting 
input/output (I/O) requests made by a user program into physical instructions understood by the 
device. The driver, in turn, responds to interrupts from the device or device controller, and reports 
status back to the user program. 

Instructions that are provided by the Perkin-Elmer Series 3200 Processors to control and 
communicate with I/O devices are privileged instructions, meaning that user programs cannot 
execute them. This is common practice in computer systems where instructions are used to 
communicate with peripheral devices. (In systems which use memory-mapped I/O, the memory 
cells that control devices are normally inaccessible to user programs, thereby yielding the same 
effect.) The main reason for the restriction on I/O control is to protect the system and the user 
from unintentional (or malicious) interference. The I/O drivers and supporting I/O subsystem 
provide the mechanisms for users to access standard devices and for new devices to be added to the 
system . 

In general, programming of I/O devices is dictated by the physical characteristics of the device and 
the needs of the user. In addition, drivers for different devices are programmed quite differently. 
However, the typical user level programmer does not want to be concerned with these differences. 
From the programmer's viewpoint, writing a line to the printer should be no different from writing 
the same line to a CRT or a disk file. This concept is called device-independent programming. It is 
also the domain of the I/O subsystem and device drivers. Device-independent programming is not 
always possible, nor is it always desirable. For example, a gapless magnetic tape is a device whose 
performance characteristics preclude device-independent programming (due to the system overhead 
in handling individual reads and writes). The gapless tape driver provides a device-specific 
interface which allows a list of several buffers to be provided in a single read or write call. 

For both the case of device-independent programming and that of a device-specific interface, the 
device driver is responsible for mapping the logical device interface as seen by the user level 
programmer into the physical device. The driver projects an interface which hides, modifies or 
passes through unchanged the idiosyncrasies of the physical device's programming characteristics. 
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1.3 BASIC INFORMATION 

To successfully implement an OS/32 device driver, the systems programmer must understand 
several related interfaces. These interfaces, discussed briefly in the following sections and in 
greater detail in subsequent chapters, are: 

• the Perkin-Elmer Series Processor 3200 I/O Architecture, 

• the OS/32 I/O subsystem architecture, 

• the programming attributes of the physical device, and 

• the logical device projected by the driver. 

1.3.1 The Perkin-Elmer Series 3200 Processor Input/Output (I/O) Architecture 

The Perkin-Elmer Series 3200 Processor I/O Architecture is the hardware framework in which all 
I/O programming is implemented. It is detailed in all of the Perkin-Elmer Series 3200 Processor 
Reference Manuals. The I/O architecture consists of definitions of the following: 

• device addressing, 

• device command and status formats, 

• I/O bus data paths, 

• instructions to control and communicate with physical devices, 

• data structures associated with interrupt processing, and 

• interaction of processor status word with external and internal interrupts. 
These definitions, and their impact on OS/32 drivers, are summarized in Chapter 2. 

1.3.2 OS/32 Input/Output (I/O) Subsystem Architecture 

The OS/32 I/O subsystem architecture is the software framework in which all device drivers 
execute. The user interface to the I/O subsystem is supervisor call 1 (SVC1), which is fully 
described in the OS/32 Supervisor Call (SVC) Reference Manual. Integrated Telecommunications 
Access Method (ITAM) drivers; i.e, network drivers such as Ethernet, Bisync and SDLC, use 
SVC15. 

The device driver interface to the I/O subsystem defines the following: 

• Data structures for controlling the interaction of the driver with the remainder of the system. 

• The general structure of device drivers, including register conventions. 

• System interface and utility routines and their register calling conventions. 
The interface is the primary subject of this document. 
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1.3.3 Programming Attributes of Physical Devices 

I/O peripheral devices are connected to a Perkin-Elmer Series 3200 Processor via a device interface 
or controller board. Each such controller has its own repertoire of supported commands and 
resulting status, and interrupt conditions. Also, correct operation of the device is often dependent 
upon a specific sequence of command and data transfers. Failure to observe this programming 
sequence will generally lead to the device failing to operate in the desired manner. 

It is the responsibility of the driver programmer to understand all of the programming requirements 
of the particular device. This information is usually defined in the appropriate device/controller 
programming reference manual. Other than the standard command and status formats and the 
sample code sequences, this information is outside the scope of this manual. 

1.3.4 Logical Devices Projected by a Driver 

As discussed earlier in this chapter, one of the primary purposes of a driver is to project a 
simplified, often device-independent view of a physical device. This simplified view is the logical 
device to which this section refers. It is the user level (SVC1) programming interface to the device. 
Unless the driver is being designed to conform to an existing Perkin-Elmer interface (e.g., a new 
CRT or disk), the definition of the logical device interface is left to the driver writer. 

The OS/32 I/O subsystem places some restrictions on this interface by the way in which it interprets 
certain fields of the SVC1 parameter block. Within these limits, the driver writers are at liberty to 
extend the interface in any direction which best accomplishes their objectives. It is the responsibility 
of the driver writer to document the logical device interface, including: 

• Function codes and options 

• Status returns 

• Extensions to standard SVC1 parameter block 
t Sequence of command occurrence 

• Buffer alignment or format requirements 

1.3.5 Including a Driver in the Operating System 

OS/32 device drivers are included in the system during the system generation (sysgen) process. 
Sysgen/32 processes system configuration statements to produce a macro level source file. This file 
is assembled and linked with standard Perkin-Elmer supplied system modules and driver libraries to 
produce an operating system image. 

Sysgen/32 and the sysgen procedures have provisions for including customized device drivers in the 
system. Specifically, the sysgen procedures search for a user driver macro library 
(USERDLIB.MLB) containing macro definitions for user-written device control block (DCB) 
structures, and a user driver object library (USERDLIB.LIB) containing bodies of user-written 
drivers in object format. 

The procedure for including a driver in the system is described in Part I, Chapter 3. 
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"CHAPTER 2 
SERIES 3200 INPUT/OUTPUT (I/O) ARCHITECTURE 

2.1 INTRODUCTION 

This chapter describes the Perkin-Elmer Series 3200 Processor I/O Architecture. Specifically, it 
covers: 

• The multiplexor (MUX) bus 

• The interaction of the program status word (PSW) with the I/O system 

• The Series 3200 Processor I/O instruction repertoire 

• The Series 3200 Processor I/O interrupt structure 

Figure 2-1 shows a detailed description of the hardware architecture on a Series 3200. 
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Figure 2-1. Hardware Configuration 
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2.2 MULTIPLEXOR (MUX BUS) 

Control over peripheral devices and communication with them is accomplished via the MUX bus. 
Even direct memory access (DMA) devices are programmed (i.e., setup) and monitored via the 
MUX bus, and are designed to notify the processor of normal or error termination via the MUX 
bus. 

The MUX bus gets its name from the fact that device addresses, device commands, device status 
and, of course, data are multiplexed on this bus. The bus consists of 16 bidirectional data lines and 
several control (from central processing unit (CPU) to controller) lines, and signal (from controller 
to CPU) lines. The control lines determine the interpretation (by the controller) of the contents of 
the data bus; i.e., device address, commands, status or actual data. The signal lines are used to 
synchronize the operation of the controller with the processor and to request service by the 
processor. 

2.2.1 Device Address 

Controllers on the MUX bus are addressed by a 10-bit device address, sometimes referred to as the 
device address. With 10 bits, it is possible to address 1,023 device addresses. In a Model 3260 
System containing an input/output processor (IOP), with certain restrictions, this number can be 
exceeded. Device address is reserved as the illegal device address. 

It is generally not possible to connect 1,023 separate devices to a Series 3200 Processor. The reason 
for this is that many device controllers use up more than one device address. For example, a disk 
controller, capable of supporting four disk drives, uses five device addresses - one for each drive 
and one common address for the controller. Communications interfaces generally require two 
addresses per communications line - one for the receive side and one for the transmit side. 

Each of the I/O instructions, discussed later in this chapter, operates on a device address. The 
device address, specified by a general-purpose register number that contains the address, is placed 
on the MUX bus data lines and the appropriate control signal is asserted. This causes the addressed 
device to become selected (and all other devices to become deselected). The processor then transfers 
commands, status or data either to or from the selected device as specified by the instruction. 

NOTE 

No two device controllers on the bus can have the same 
address. Addresses on an IOP can be the same as on the 
CPU or another IOP, with restrictions on diagnostics. 

2.2.2 Device Commands 

The processor controls the state of a device controller using device commands. A command is an 
8-bit datum that is passed to the (selected) controller via the MUX bus data lines. Commands are 
differentiated from data by a bus control line. An 8-bit command allows 256 unique commands to 
be specified. As commands are normally bit-encoded (i.e., bits are assigned specific meaning), the 
effective number of meaningful commands for a controller is usually much less than 255. 
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Some device controllers may require a larger command space than afforded by the standard 8-bit 
command. This can be done in one of several ways: 

• the controller might use multiple device addresses, with commands to the different addresses 
interpreted differently, or 

• the controller might interpret all data written to one or more device addresses as commands, and 

• a specific command bit could condition the controller to accept one or more subsequent data 
bytes or halfwords (16 bits) as commands. 

By convention, the first two. bits of a command byte are assigned a standard meaning. Bits and 1 
control the device's interrupt flip-flop. Bit is the DISABLE command and bit 1 is the ENABLE 
command. See Figure 2-2 for an illustration of these bits. (For reference purposes, Figure 2-3 
shows the SELCH command.) 
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Figure 2-2. Standard Device Command (SELCH not included) 
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Figure 2-3. SELCH Command 



If DISABLE is set and ENABLE reset (10 2 ), interrupts are disabled but queued at the interface. 
With DISABLE reset and ENABLE set (01 2 )» interrupts (including a queued interrupt) are allowed 
to be passed to the processor. If both DISABLE and ENABLE are set (l^). interrupts are 
disarmed; interrupt conditions will be ignored by the controller. The combination of both DISABLE 
and ENABLE reset (00_) has no effect on the state of the controller's interrupt logic. This is useful 
for commands that otherwise affect the state of the controller, without changing the interrupt state. 

The remaining six bits of the command byte are device specific. Not all are necessarily defined for 
all controllers. The actual meaning of these bits should be documented in the appropriate device 
controller's programming reference manual. This information is mandatory for writing a driver for 
the device. 
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2.2.3 Device Status 

The processor senses the state of a device controller by accessing an 8-bit device status. The status 
byte is requested from the (selected) device by asserting the appropriate MUX bus control line. 
The controller places the status on the bus data line. As with commands, status bytes are usually 
bit-encoded. Devices that require more than eight bits of status typically resort to the same types of 
mechanisms described in Section 2.2.2. 

Certain bits of the device status are assigned default meaning by convention. Figure 2-4 illustrates 
default device status settings. 
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Figure 2-4. Standard Device Status 



Bit 4 is interpreted as the busy (or not ready) bit; i.e., when set, the device is busy. For input 
devices, this typically means that no data is available at the interface. For output devices, it means 
that the controller is not ready to accept further data. If the device supports program detection of 
power-up condition, this is normally assigned to bit 7. If set, it indicates device unavailable - this is 
a much softer convention than the busy bit above. 

Finally, bit 5 is usually defined as the logical OR of bits through 3. Bit 5 is called the examine 
bit. The reason for this is as follows: when the processor performs a sense status operation, bits 4 
through 7 of the status are copied into the PSW condition code. Conditional branch instructions are 
then able to test these bits directly. Bits through 3 cannot be tested in a like manner. Therefore, 
the convention was developed that bit 5 would be set whenever any one or more of bits through 3 
are set. Thus, with a single branch instruction, one can test bit 5 (which is copied to the overflow 
condition code bit) and branch off to a routine to examine bits through 3 one-by-one. 

Except for the busy bit (bit 4), which is an almost universal convention and the examine bit, which 
is nearly so, the assignment of status bits is device specific. The required action response of the 
processor or driver to the status conditions is also device specific. This information should be 
documented in the appropriate device/controller programming reference manual, and is required to 
write a driver for the device. 

2.2.4 Data 

The MUX bus supports data transfers in units of 8 or 16 bits. This is called byte and halfword 
mode, respectively. The data transfer width is a characteristic of the physical device. Most Perkin- 
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Elmer supplied devices are byte-oriented. The exceptions to this tend to be process I/O devices such 
as analog-to-digital or digital-to-analog converters and digital I/O modules. Also, some newer tape 
and disk interfaces use half word transfers for command and status information, as outlined in 
Section 2.2.2. 

2.3 PROGRAM STATUS WORD (PSW) AND MACHINE STATES 

The PSW is a 64-bit internal register that controls and records the current state of a Series 3200 
Processor and consists of two 32-bit fields. One field, the location counter (LOC), always contains 
the address of the next instruction to be executed. The other field, shown in Table 2-1, contains 
processor status/control information. When an I/O device interrupts the processor, the current 
PSW /LOC is saved and a new PSW /LOC is derived based on information supplied by the 
interrupting device. Where the old PSW is saved and how the new one is derived are discussed in 
Section 2.5. Whether or not an interrupt is possible, is controlled by two bits in the PSW. Bits 17 
and 20 control the I/O interrupts as shown in Table 2-1. 



TABLE 2-1. PSW STATUS FIELD FOR PERKIN-ELMER SERIES 3200 PROCESSORS 



BIT 17 


BIT 20 


EXPLANATION 





1 

1 



1 



1 


All I/O Interrupts disabled 

Interrupts enabled at higher 

priority levels 

Interrupts enabled at all 

priority levels 

Interrupts enabled at current 

and higher priority levels 



When bit 17 is 0, the processor is considered to be in the interrupt service state. This is the most 
privileged state of the machine - the program executing in interrupt service state has complete 
control of the processer. 

PSW bits 24 through 27 are closely related to the I/O architecture. These bits select one of eight 
register sets on the Series 3200 Processors (one of two sets on the Model 7/32 and some Model 8/32 
Processors). Register sets through 3 are tied to the four I/O interrupt priority levels. This is 
discussed further in Section 2.5.1, External Interrupts. 

PSW bit 22 controls the system queue service (SQS) interrupt. SQS is a software or internal 
interrupt as described above. When bit 22 is enabled, the processor is considered to be in a reentrant 
or eventable state. When bit 22 is reset, the system is in a nonreentrant or, possibly, event service 
state. 
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Finally, PSW bits 28 through 31 contain the condition code. The condition code reflects the results 
of the most recent arithmetic or I/O operation. It is also setup on an interrupt as discussed in the 
section on interrupts. 

The machine states associated with driver routines are the nonreentrant system state, the event 
service state and the interrupt service state. System states are described in detail in Appendix B. 

2.4 INPUT/OUTPUT (I/O) INSTRUCTIONS 

Perkin-Elmer Series 3200 Processors I/O instructions control the transfer of commands, status and 
data between the processor and the device controllers. They are defined in detail in any Perkin- 
Elmer Series 3200 Processor reference manual. An important point to note is that whenever any of 
the I/O instructions are issued, the processor waits for the addressed device to respond with a 
synchronization signal (called SYNC). To prevent the processor from waiting indefinitely (for a 
nonexistent or malfunctioning device), the instructions will time-out after a brief interval has 
elapsed. This condition is called a FALSE SYNC. The time interval varies from processor to 
processor, but it is on the order of 15-30/is When an I/O instruction times-out, the overflow bit in 
the PSW condition code is set. This is known as false sync condition. 

2.4.1 Output Command (OC) Instructions 

The OC instruction causes an 8-bit device command to be transferred to the addressed device. Like 
all I/O instructions, this command has two formats - a memory (RX) format, and a register (RR) 
format. 



Example: 



OC R1,A(X1) RX format 
OCR R1,R2 RR format 

In both formats, the Rl contains the device address in bits 22 through 31. In the RX format, the 
byte value in memory at A(X2) is the command byte to be transferred. In the RR format, the 
command byte is located in bits 24 through 31 of the register specified by R2. Note that this 
instruction does not have an immediate format; attempting to use an immediate format is a common 
mistake made in drivers. An output command is often the first instruction issued to a device in a 
driver. This is normally done to place the device in a known state. It is customary to test for 
FALSE SYNC immediately after this initial command. 
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Example: 



LHL R2 , DCB . DN (RD) Get device address 

OC R2 / INITCMD Issue Initial command 

BO NONESUCH FALSE SYNC - no such device 



2.4.2 Sense Status (SS) 

The SS instruction requests an 8-bit device status byte to be transferred from the addressed device. 
This instruction has both an RX format and an RR format. 



Example: 

SS R1,A(X2) RX format 
SSR R1,R2 RR format 



In both formats, Rl contains the device address in bits 22 through 31. In the RX format, the status 
byte is returned to the memory byte specified by A(X2). In the RR format, the device status is 
returned to bits 24 through 31 of the register specified by R2. When an SS (or SSR) instruction is 
executed, the low -order four bits of the status are copied into the condition code bits of the PSW. 
While this makes normal tests (e.g., for busy) quite efficient, it makes testing for FALSE SYNC 
somewhat more complicated after a sense status. This is because the PSW overflow condition code 
may be set for reasons other than FALSE SYNC. In general, it is only necessary to test for FALSE 
SYNC once in a driver. It is recommended that this be done after an OC rather an SS instruction. 

2.4.3 Write Data (WD)/Write Data Halfword (WH) 

There are two types of write instructions. WD transfers an 8-bit data byte to the addressed device. 
WH transfers a 16-bit data halfword to the device. Both types of write instructions come in RX and 
RR formats. 
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Example: 



WD R1,A(X2) Write data RX format 
WDR R1,R2 Write data RR format 

WH R1,A(X2) Write half word RX format 
WHR R1,R2 Write half word RR format 



In all these instructions, bits 22 through 31 of the register specified by Rl contain the device 
address. RX transfers the contents of the memory byte specified by A(X2). RR transfers bits 24 
through 31 of the register specified by R2. WH RX transfers the contents of halfword specified by 
A(X2). This address must be halfword-aligned (i.e., even). The RR format of WH transfers the 
lower halfword (bits 16 through 31) of the register specified by R2. For all write instructions, the 
addressed device must support output and must not be busy. Otherwise, the results are undefined. 

2.4.4 Read Data (RD)/Read Data Halfword (RH) 

There are two types of read instructions. RD transfers an 8-bit data byte from the addressed device, 
and RH reads a 16-bit data halfword. Both types of read instructions have both RX and RR 
formats. 



Example: 

RD R1,A(X2) Read data RX format 

RDR R1,R2 Read data RR format 

RH R1,A(X2) Read halfword RX 

RHR R1,R2 Read halfword RR 



In all four instructions, the device address is contained in bits 22 through 31 of the register specified 
by Rl. RX reads a data byte into the memory byte specified by A(X2). RDR reads the data byte 
into bits 24 through 31 of the register specified by R2. Bits through 23 of register R2 are cleared 
to zeros. RH reads 16 bits of data into the memory halfword specified by A(X2). This address must 
be halfword-aligned (i.e., even). RHR reads the data halfword into bits 16 through 31 of register 
R2. Bits through 15 of the register specified by R2 are cleared to zeros. For all of the read 
instructions, the addressed device must support input and must not be busy. Otherwise, the results 
are undefined. 
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2.4.5 Other Input/Output (I/O) Related Instructions 

There are two additional instructions that are part of the I/O architecture that do not perform any 
I/O on the MUX bus. These are the simulate interrupt (SINT) and the simulate channel program 
simulate channel program instructions. The SINT instruction is an immediate (RI) format. 



Example: 

SINT R1,I(X2) Simulate Interrupt Rl 
SINT I (X2) Simulate interrupt 

The SINT instruction causes the processor to execute the same internal sequence as if an interrupt 
were received from the device whose address is specified by I(X2). The contents of Rl, if present, 
specifies the priority level at which the interrupt is simulated. If Rl is not present, the processor 
defaults to level 0. The least significant ten bits of the second operand are presented to the interrupt 
handler as a device number. The device number is used to index to the interrupt service pointer 
table (ISPT), simulating an interrupt from an external device. Interrupts and priority levels are 
described in the next section. 

The simulate channel program instruction has only an RX format. 
Example: 

SCP R1,A(X2) Simulate channel program 

This instruction causes the processor to execute an auto driver channel control block (CCB) 
specified by the A(X2) operand. Data is moved between Rl and the memory buffer specified by the 
CCB. The auto driver channel is described in a subsequent section. 

2.5 INTERRUPTS 

The Series 3200 Processor I/O Architecture, in the context of OS/32 device drivers, supports two 
classes of interrupts. External interrupts are those interrupts that are generated by devices on the 
MUX bus. They occur asynchronously from instruction execution and, except for a few interruptible 
instructions, they are only recognized between instruction executions. 

Internal interrupts, on the other hand, are generated by the Series 3200 Processor microprogram. 
They occur synchronously with instruction execution. The supervisor call (SVC) and system queue 
service (SQS) interrupts, described in a later section, is of particular importance to the OS/32 I/O 
subsystem and device drivers. 
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2.5.1 External Interrupts 

All external interrupts occur via the MUX bus. A device controller requests service by asserting its 
attention signal. A controller may be connected to one of four attention lines. The four attention 
lines are arranged in four priority levels numbered through 3. Level is the highest priority level; 
3 is the lowest. To be sensed, interrupts must by enabled. Interrupts are enabled by a combination 
of the PSW bits 17 and 20 and the currently selected register set (bits 24 through 27). See Section 
2.4 for a discussion of the PSW bits 17 and 20. 

When the processor recognizes an interrupt at level n, the following actions occur: 

1. The processor acknowledges the interrupt by asserting a MUX bus control line. This causes 
the device to return its device address on the MUX bus data lines. Also, the interrupting 
device becomes selected. 

2. The processor saves the current PSW and location counter (LOC) and generates a new PSW 
that selects the register set equal to the interrupting priority level. Higher level interrupts 
remain enabled (i.e., if the interrupting level is not level 0). The old PSW and location are 
saved in registers and 1 of the selected set. 

3. The processor saves the address of the interrupting device in register 2 of the new set. It then 
requests the current status of the selected (interrupting) device and places this status byte in 
bits 24 through 31 of register 3 of the new set. All other bits are zeroed. 

4. The address of the channel command block is placed in register 4 of the selected register set 
(if a CCB is being used; see further discussions of the ISPT in the Chapter 3. 

5. The LOC of the new PSW is determined from the contents of an external interrupt vector 
table called the ISPT. The ISPT is discussed in the next chapter. 

2.5.1.1 Interrupt Service Pointer Table (ISPT) 

The ISPT is a vector table for external service. For all Series 3200 Processors and for the Models 
7/32 and 8/32, ISPT is a table of halfword (16-bit) pointers located at physical memory address 
X*D0\ (It is sometimes referred to as the "Dog-Zero" Table.) ISPT is indexed by twice the device 
address of the interrupting device. Because each entry is only 16 bits wide, the address must be 
within the first 64kB of physical memory. 

For the Series 3200 IOP associated with the Model 3260MPS system, the ISPT is a fullword table. It 
can be located anywhere in physical memory. It is located via a fullword pointer in the I/O 
processor block (IPB). Because it contains fullword entries, the addresses it contains can be 
anywhere in physical memory. The following paragraphs refer to ISPT entries and are equally valid 
for both the fullword IOP ISPT and the halfword CPU ISPT. 

If the ISPT entry for a particular device is even (low-order bit = 0), then the entry is the address of 
the first instruction of an interrupt service routine (ISR). This address becomes the location counter 
(LOC) for the new PSW. (Immediate interrupt service is discussed in the next section.) If the ISPT 
entry for a device is odd (low-order bit = 1), then the entry is the address +1 of an auto driver 
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CCB. (Note: this is the normal case for some OS/32 device drivers. CCBs are only for common 
drivers; disk and tape drivers do not use them.) The CCB is accessed by the processor's microcode. 
Depending on the contents of the CCB, the interrupt might be serviced completely within 
microcode; or the LOC for the new PSW might be loaded from a field in the CCB. The auto driver 
channel is discussed in a later section. 



Figure 2-5 shows the ISPT for a CPU with both immediate interrupts and CCBs. 
at X'DO* on all processors except IOPs. For IOPs ISPT may be anywhere. 



Note that ISPT is 
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Figure 2-5. The ISPT 
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2.5.1.2 Immediate Interrupt Service 

NOTE 
Immediate interrupt service is generally not useful in 
the design of custom I/O drivers. All such drivers 
require the use of the channel command block and at 
least minimal auto driver channel operation. 
Immediate interrupts are used only in certain operating 
system time-keeping operations. 

An immediate interrupt occurs if the ISPT entry for the interrupting device is even. Here the entry 
is the first address of an ISR. For all 3200 Processors, the first instruction of the ISR must be in 
the first 64kB of physical memory. (For an IOP, the ISR can be anywhere in physical memory.) 

On entry to the ISR, the processor initializes registers through 3 of the newly selected register set 
(= interrupt priority) as follows: 



TABLE 2-2. REGISTER CONTENTS ON ENTRY TO ISR 



REGISTER 


CONTENTS ON ENTRY INTO ISR 



1 
2 
3 


Old PSW status (of interrupted program) 
Old LOC 

Interrupting device's address 
Interrupting device's status 



While the hardware imposes no such restriction, OS/32 requires that ISRs restrict their register 
usage to registers through 7. This is necessary because the nonreentrant service state uses registers 
8-F on set 0. If it can be guaranteed that the ISR will execute in register sets 1, 2 or 3, this 
restriction is not required. Failure to observe this restriction in an OS/32 driver will result in 
system failure. Also, registers through 2 are usually preserved throughout an ISR. An ISR exits 
(back to the interrupted program) by loading the old PSW from registers and 1, i.e., 



LPSWR EO 
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NOTE 

It is common practice to refer to registers from within an 
ISR as En, where n is the register number. This is to make 
clear that the ISR is executing in an executive register set; 
i.e., 0, 1, 2 or 3. 

2.5.1.3 Auto Driver Channel 

The auto driver channel is a feature of all Perkin-Elmer Series 3200 Processors. It is, in effect, a 
built-in ISR. Under the control of the processor's microcode and as directed by the contents of a 
CCB, discussed below, the auto driver channel is capable of servicing a device interrupt completely 
within the processor's microcode. 

The auto driver channel supports either byte or half word devices. ISRs for halfword devices 
(RH(R)/WH(R)) must be supplied in assembly language. 

The auto driver channel supports the following features: 

• Read (or write) to/from a memory buffer with automatic entry into an ISR routine within the 
driver full/empty. 

• Automatic device status checking on each interrupt with entry into the ISR if specified status bits 
are set. 

• Optional automatic buffer switch on buffer full/empty with concurrent entry into ISR. 

• Optional redundancy check generation (longitudinal or cyclic mod 12 or mod 16). 

• Optional character set translation "on-the-fly" with special character recognition (e.g., in support 
of communications protocols). Recognition of special characters causes a specified ISR to be 
entered. 

• Optional no execute mode: direct, unconditional entry into the specified ISR. (This is the mode 
most commonly used in I/O device drivers). Note that the PSW condition code reflects reason 
for entry into the ISR: no execute, buffer full/empty, switch, or status check. 

The data structures associated with the auto driver channel are shown in Figure 2-6. 

NOTE 

CCB.DCB is set at sysgen time. CCB.XLT may be set 
at sysgen time or by driver. All other entries are set by 
driver. 



48-190 F00 R00 2-13 



ISPT 



BUFFER "8" 




*4 FOR 3200 IOP 



E0, E1 = OLD PSW, LOC 
E2 = DEV ADDRESS 
E3=DEV STATUS 
E4 « CCB ADDRESS 



-AV- 



-SV 



TRANSLATION 
TABLE 



1 




XCH 


1 




XCH 


1 




XCH 





A0SR1/2 


1 




XCH 



J 



ISR 



LPSWR E0 



Figure 2-8. Auto Driver Control Structures 

The auto driver channel is invoked by an odd entry (low-order bit set) in the ISPT. This entry is 
the address +1 of the CCB. The CCB is described in the next section. 

2.5.1.3.1 Channel Control Block (CCB) 

The CCB, as defined by the Series 3200 Processor I/O architecture, is 22 bytes long. (For the Series 
3200 IOP, it is optionally 24 bytes long, thereby providing for a fullword ISR address.) The CCB 
contains the following fields: 

• a channel control word (CCW), which specifies the desired operations and options, 

. two pairs of buffer control fields: (LB0,EB0) for buffer and (LB1.EB1) for buffer 1, 

• the redundancy check accumulator (CW), 

• the translation table Address (XLT), 

• the ISR subroutine address (SUBA), 

. the address of the associated device control block (DCB) (used for access into the OS/32 I/O 
subsystem by the ISRs.) 

These fields are initialized by a device driver before starting the device or before issuing a simulate 
channel program instruction. The SCP instruction, described in Section 2.4, acts upon a specified 
CCB and simulates the actions that would occur for a device interrupt. But, instead of transferring 
data to/from a device, data is transferred between memory and the register specified in the simulate 
channel program instruction. 
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2.5.1.3.2 Channel Control Word (CCW) 

The CCW is the operation code or function code of the CCB. The CCW specifies what operation is 
to be performed and with what options. The format of the CCW is shown in Figure 2-7. 






1 


2 3 4 5 


6 


7 


8 


9 


10 11 


12 


13 


14 


15 


Status Mask 

Mill 1 


E 


X 


RC 

1 


B 


W 


T 


F 



Where: 
E(8) 



X(9) 

RC (10-11) 



Figure 2-7. Channel Control Word 



1 = full autodriver channel control enabled 

= always execute ISR indicated by CCB.SUBA; ignore bits 10-15 

1 = CCB.SUBA is a fullword (not fully supported yet) 

= CCB.SUBA is a halfword (currently used by all drivers) 

00 = LRC parity check only 

01 = Bisync CRC 

10 = not defined 

11 = SDLC CRC 



B (12) 


= use buffer 




1 = user buffer 1 


W (13) 


= READ mode 




1 = WRITE mode 


T(14) 


= no translation 




1 = translation enabled 


F(15) 


= normal mode 




1 = "fast" mode 



NOTE 

Always use buffer 0; "no translation" must be used for 
halfword device, as well as no parity check. 

The status mask of the CCW occupies bits through 7. On every channel operation (i.e., each 
device interrupt with the CCW execute bit set), the device status is logically AND-tied with the 
status mask in the CCW. This is simply a test and does not alter the status mask or the device 
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status. If the results of the test is nonzero, the channel operation is aborted and the ISR specified by 
the SUBA field is entered. The L bit of the new PSW condition code is set to indicate the reason for 
the ISR entry. 

The CCW execute bit (CCWEX) is located at bit 8. CCWEX controls the operation of the channel. 
If the bit is 0, the channel enters the specified ISR SUBA directly. No other channel operation is 
executed, including the status check. The new PSW condition code is set to 0. If CCWEX is set, the 
channel operation defined by the remainder of the CCW is executed. This may or may not result in 
the ISR subroutine's being entered. 

The extended ISR address bit 9 (CCWXISR) is defined only for the Series 3200 IOP associated with 
the Model 3260MPS. It indicates that the ISR (SUBA) field is a fullword rather than a halfword. 
For reasons of compatibility, this bit is not used by standard OS/32 drivers. 

Two CCW bits (10 through 11) control the optional redundancy check generation. Three types of 
redundancy check are supported as listed in Table 2-3. 

TABLE 2-3. REDUNDANCY CHECKS 



RC BITS 




1 

1 



RC TYPE 



Longitudinal redundancy check (LRC) 
BISYNC cyclic redundancy check (CRC12) 
Reserved - illegal 
SDLC cyclic redundancy check (CRC16) 



Redundancy check sums are calculated and accumulated in the check word CCB field as each 
character is read or written. The details of the redundancy check calculation are given in the 
appropriate processor reference manuals. (Note that redundancy check generation is not performed 
if the CCW fast bit is set.) 

The buffer select bit (CCWB1) is located at bit 12 and controls which of the two CCB buffers (0 or 
1) is used by the channel. When a device interrupt causes a data transfer that results in a buffer 
overflow (full/empty), this bit is complemented, causing a buffer switch. At the same time, the 
specified ISR SUBA is entered with the new PSW condition code G bit set to indicate the reason for 
entry to the ISR. Upon the next interrupt after a buffer switch, the channel proceeds to use the 
alternate CCB buffer as specified by the complemented CCW buffer select bit. It is the 
responsibility of the driver software to ensure that the alternate buffer is setup correctly. (Note that 
buffer switching is not performed if the CCW fast bit is set. In that case, only buffer is used.) 

The CCW read/write bit (CCWRD/CCWWR) located at bit 13 controls the direction of data 
transfer. If reset (0), the channel performs a read operation; if set, a write is attempted. It is the 
responsibility of the device driver to ensure that the setting of this bit agrees with the current mode 
(input or output) of the device. 
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The CCW translation bit (CCWTL) at bit 14 enables optional character set translation and special 
character trapping. Translation and the translation table format are described in Section XX. (Note 
that translation is not performed if the CCW fast bit is set.) 

The CCW fast bit (CCWFST), located at bit 15, disables the optional functions when set. These are 
buffer switching, translation and redundancy check generation. This provides for more efficient 
interrupt service (in terms of CPU time) for devices that do not require the optional functions. 
When the fast bit is set, the channel bypasses the checks for the optional function bits. 

2.5.1.3.3 Channel Control Block (CCB) Buffers 

The auto driver channel provides for two data buffers with optional automatic buffer switching. 
There are two fields in the CCB that control each buffer. 

Buffer n (n = or 1) is described to the channel by its end address (EB«) and its length (LBn). 
(The end address is defined as the address of the last byte of the buffer and must be odd for 
halfword transfers.) Because the end address is a fullword field, the buffer can be located anywhere 
in physical memory. 

The buffer length field is defined as the buffer start address minus the end address. Thus, except for 
the case of a single byte transfer, the Buffer Length will be a negative value. For each data transfer, 
the channel increments the length field by one (for byte) or two (for halfword). When the value 
becomes positive, the last character has been transferred. Note that the sum of the end address and 
the buffer length yields the address of the next character to be transferred. 

2.5.1.3.4 Check Word 

The CCB check word is a two-byte field where the optional redundancy check is accumulated. It is 
normally initialized to or -1 before transferring a buffer, depending on the communications 
protocol. 

The check word is updated as each character is read or written. On output, the resulting check 
word is usually transmitted after the last data character. On input, it is customary to cease 
accumulation after the input termination character is recognized. Then the check word calculated by 
the sender is read and compared to that calculated by the channel. A difference generally indicates a 
data transmission error. (Check words are used almost exclusively in data communications drivers.) 

2.5.1.3.5 Translation Table 

The CCB translation table pointer is used only if the CCW translate bit is set (and the fast bit is 
reset). This CCB field contains the address of a table of halfword entries. This is illustrated in 
Figure 2-5. When translation is enabled, the channel accesses the table using twice the data byte as 
the index. If the high-order bit of the addressed entry is set, then the low-order byte contains the 
translated character (XCH in Figure 2-5). 

If the high-order bit of the entry is reset, then the remaining 15 bits of the entry contain one-half the 
address of a special character handling routine. The entry is doubled and the ISR subroutine at the 
resulting address is entered exactly as if the CCW execute bit has been reset (i.e., new PSW 
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condition code = 0). 

The translation table can be used for character set translation (e.g., ASCII to EBCDIC, or vice 
versa); or for recognizing special characters of communications protocols. 

2.5.1.3.6 Interrupt Service Routine (ISR) Subroutine Address (SUBA) 

The CCB ISR (SUBA) field contains the address of an assembly language ISR that handles all error 
and normal termination conditions. In addition, this ISR is entered when the CCW execute bit is 
reset. For all 3200 Processors except the IOP, this is a halfword field. Thus, the first instruction of 
the ISR must be within the first 64kB of physical memory. For the IOP, this field may optionally be 
a fullword if the CCW extended ISR address bit is set. 

Entry to the specified ISR is exactly the same for an immediate interrupt ISR except for the 
following two items: 

1. The new PSW condition code indicates the reason for entry as shown in Table 2-4: 

2. In addition to the contents of registers through 3, which are the same as for an immediate 
interrupt, register 4 contains the address of the CCB itself. This property is most important to 
OS/32 drivers as it provides a dynamic link to a data structure associated with the interrupting 
device, allowing reentrant/sharable drivers to be written. 



TABLE 2-4. PROGRAM STATUS WORD CONDITION CODES 



Condition Code 











1 




1 




Explanation 



No Execute or Translation Table 
Device Status Check 
Buffer End 



2.5.2 Internal Interrupts 

The Perkin-Elmer Series 3200 Processors support a number of internal interrupts. Two of these 
internal interrupts are of particular interest in understanding the OS/32 I/O subsystem and device 
drivers. These are: 

• the supervisor call (SVC) interrupt, and 

• the system queue service (SQS) interrupt. 

Other internal interrupts are associated with fault conditions, such as illegal instructions, address 
alignment faults or arithmetic faults. If any of these faults occur within a driver, the system will 
crash. 
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All internal interrupts occur synchronously with instruction execution; and they are serviced by a 
common method. A new PSW and LOC are loaded from a dedicated location in low memory. 
Each of the internal interrupts cause the PSW and LOC to be loaded from a different location. The 
old PSW and LOC are stored in registers 14 and 15 of the register set selected by the new PSW. 
Other registers (13, 12, etc.) are loaded with information dependent on the type of internal 
interrupt. 

NOTE 

On the Series 3200 IOP, the new PSW and LOC for 
internal interrupts are located at dedicated locations in 
the I/O processor block (IPB). Also, in the IOP, there 
is no SQS interrupt. The function of SQS is provided by 
the IOP synchronous interrupt service (SIS). These 
concepts and other differences between a Series 3200 
Processor and the Series 3200 IOP are covered in 
Chapter 8. 

2.5.2.1 Supervisor Call (SVC) Interrupt 

The SVC interrupt is invoked by the SVC instruction. The SVC is the primary instrument for 
invoking operating system services. The SVC instruction selects one of 16 service routines (0 
through IS) and specifies the address of a parameter block (or parameter list). 

The new PSW for all 16 SVC service routines is loaded from the same dedicated memory location. 
The new LOC is loaded from a table of halfword service routine addresses, indexed by the SVC 
number (0 through 15). Because the table entries are only halfwords, the first instruction of service 
routines must reside in the first 64kB of physical memory. The new PSW and LOC values are set 
up by the operating system in control of the processor. Usually, the new PSW allows privileged 
instructions to be executed and selects a new register set so that the register set of the caller is not 
corrupted (e.g., by the PSW and LOC). 

In addition to the old PSW and LOC which are saved in registers 14 and 15, the SVC internal 
interrupt loads the address of the SVC parameter block into register 13 of the new register set. 
Some SVCs may choose to interpret this address as an immediate value. 

2.5.2.2 System Queue Service (SQS) 

The SQS internal interrupt is the primary mechanism for synchronizing asynchronous events (such 
as termination of an I/O operation) with the more orderly sequence of events within an operating 
system. The system queue is a standard Perkin-Elmer circular list structure accessed by the Series 
3200 Processor LIST instructions (ATL, ABL, RBL, RTL). The address of the system queue is 
stored in a dedicated memory location. 

The system queue is examined by the processor whenever a new PSW that enables the SQS 
interrupt is loaded. If the queue is nonempty, an SQS internal interrupt occurs. A new PSW and 
LOC are loaded from a dedicated location and the old PSW and LOC are saved in registers 14 and 
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15 of the new register set. Register 13 is loaded with the address of the system queue. The SQS 
routine must remove and service entries from the system queue. A queue entry is the address of an 
event coordination leaf that contains the address of a service subroutine and argument values for 
that routine. 



2-20 48-190 F00 R00 



CHAPTER 3 
INPUT/OUTPUT (I/O) PROGRAMMING METHODS 

3.1 INTRODUCTION 1 

3.2 PROGRAMMED INPUT/OUTPUT (I/O) 2 

3.2.1 Status Loop Monitoring 2 

3.2.2 Interrupt-D riven Programmed Input/Output (I/O) 4 

3.2.2.1 Immediate Interrupt Service 5 

3.2.2.2 Auto Driver Channel Programming 6 

3.3 DIRECT MEMORY ACCESS (DMA) PROGRAMMING 9 

3.3.1 The Selector Channel (SELCH) 9 

3.3.2 Programming the Selector Channel (SELCH) 10 



CHAPTER 3 
INPUT/OUTPUT (I/O) PROGRAMMING METHODS 



3.1 INTRODUCTION 

Device drivers can transfer data between the Perkin-Elmer Series 3200 Processor/memory and I/O 
devices by one of two ways: 

• Programmed I/O where the processor is involved in the transfer of each byte (or halfword) of 
data. 

• Direct memory access (DMA) I/O where the processor sets up a selctor channel (SELCH) that 
performs byte (or halfword) transfers directly between memory and device controllers over the 
DMA bus. 

The mode used is usually based on the hardware configuration and the transfer speed of the device. 
Faster devices such as (hard) disks and high performance magnetic tapes can only use DMA to 
achieve their maximum performance. Also, DMA devices tend to be block transfer devices rather 
than single character interaction devices. 

Slower or more interactive devices, or devices whose only purpose is to generate interrupts (such as 
a periodic timer) generally use programmed I/O. Regardless of which (programmed I/O or DMA) 
mode of data transfer is used, device drivers can control and monitor the device (or SELCH) by one 
of two programming methods: 

• Status-Loop Monitoring - the processor loops on device status. Data is transferred when the 
device is not busy. Transfer is terminated when all data is transferred or an error condition 
occurs. Most OS/32 device drivers should never use status loop I/O since it requires that the 
CPU be dedicated to the I/O operation. Status loop I/O is used only in stand alone routines such 
as diagnostics. 

• Interrupt-Driven I/O - the processor sets up the interrupt service pointer table (ISPT) vector for 
the driver and enables device interrupts. The device interrupts the processor; when busy the 
processor stops and/or an error status is raised (device-specific). The interrupt service routine 
(ISR) transfers a byte/halfword of data if the device is not busy and no error has occurred. 
Transfer is terminated when all data is transferred or an error occurs. 

The descriptions above specifically describe methods of monitoring programmed I/O. For DMA, the 
processor loops on SELCH status or waits for the SELCH to interrupt to indicate that the transfer is 
complete. Meanwhile, the SELCH is, itself, performing what is essentially a status monitoring loop 
on the device under its control. 
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3.2 PROGRAMMED INPUT/OUTPUT (I/O) 

This section describes the basic sequences of programmed I/O for the Series 3200 Processor I/O 
architecture. Sample code sequences are presented and analyzed for status loop monitoring and 
interrupt-driver I/O. Both immediate interrupt service and auto driver channel are covered. 

3.2.1 Status Loop Monitoring 

Status loop monitoring is the most basic form of I/O programming. It is simplest to explain and to 
understand. It also forms the basis for both interrupt driven programmed I/O and DMA I/O. 

While status loop monitoring is the simplest form of I/O, it requires that the processor be dedicated 
to the I/O programming during the entire data transfer or other I/O functions. For this reason, it is 
normally used only in stand-alone programs such as hardware test programs or operating system 
boot loaders. Device drivers in an operating system normally use interrupt-driven I/O (discussed in 
Section 3.2.2). Generally speaking, status loop monitoring is not appropriate for OS/32 I/O drivers. 

There is one situation where an OS/32 device driver uses a status loop I/O rather than interrupt- 
driven I/O. This is the case where the device has a sufficiently high data transfer rate that is nearly 
always ready (i.e., not busy) from the processor's viewpoint. It is more efficient in terms of both 
central processing unit (CPU) use and elapsed time to perform the data transfer in an interruptable 
status loop rather under interrupt control. A high-speed buffered line printer with a parallel 
interface is one such device. 

In the examples below, the following preconditions are assumed: 



• Register zero (R0) is a scratch register. 

• Register one (Rl) contains a buffer start address. 

• Register two (R2) contains the constant 1 . 

• Register three (R3) contains the buffer end address. 

• Register six (R6) contains the device address. 

• SETUPDEV is a memory location that contains a device command byte. 

• FALSYNC and IODONE are external program labels. 



Note that registers 1 through 3 are setup for a BXLE loop. 
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The first example illustrates a simple sense status loop to read a sequence of data bytes into a 
memory buffer until the buffer is full: 



OC R6,SETUPDEV Command device 





BO 


FALSYNC 


STATLOOP 


SSR 


R6,RO 




BCS 


STATLOOP 




RD 


R6,0(R1) 




BXLE 


Rl, STATLOOP 




B 


IODONE 



False Sync: Device nonexistent 
Sense device status info RO 
Sets CC carry if busy 
Not busy: read a byte 
Increment Rl and loop 
until buffer is full 



The sense status (SSR) instructions copy the low 4 bits of device status into the program status word 
(PSW) condition code. The branch on carry short (BCS) instruction tests the busy status that 
appears in the carry bit of the condition code. This example loops on busy, i.e., it branches back to 
the SSR instructions until busy drops. 

Each time busy drops, the BCS falls through and the read data instruction reads a byte of data from 
the device and places it in memory of the address contained in Rl. The BXLE instruction 
increments Rl (by the value in R2) and compares it to the value in R3 (end address). If the update 
buffer address in Rl is less than or, equal to (LE) the end address, the BXLE branches back to loop 
on busy. 

A bad status causes the status loop to be exited. At label EXAMINE, the device status in RO is 
tested bit by bit. The symbols STAT.XXX, STAT.YYY are assumed to be equated to the various 
device status bits. Labels ERRXXX, ERRYYY are program labels that handle the named error 
conditions (XXX or YYY). 

Often it is desirable to limit the number of times that the sense status loop is executed. This is 
called a limited sense status loop. It is used to provide a safety exit if busy does not drop within an 
expected time interval. The final example assumes that the symbol SSLIMIT is equated to the 
maximum number of times that the sense status loop should be executed: 
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LI R4,SSLIMIT Set up loop limit 

STATLOOP SIS R4,l Decrement loop limit 

BNP TIMEOUT Exit when limit exhausted 

SSR R6,R0 Sense device status into RO 

BO EXAMINE Exit if errors 

BCS STATLOOP Loop if busy 



In a limited sense status loop, one usually desires to loop for a specific time interval rather than a 
specific number of times. The loop limit is a simple way to terminate a loop after some time 
interval. The actual time interval is the product of the loop limit and the sum of the execution times 
of the instructions in the loop. This latter value varies from processor to processor so that a 
minimum value (for the fastest processor) is usually assumed. 

3.2.2 Interrupt-D riven Programmed Input/Output (I/O) 

Interrupt-driven I/O is the most frequently used I/O programming method in OS/32 device drivers. 
The use of interrupts allows the processor to be used for other tasks while the I/O is in progress, 
rather than waiting in a sense status loop. Interrupt programming is generally viewed as more 
complex than status loop monitoring because the driver relinquishes control of the processor while 
waiting for an interrupt. Thus, it must save its context (e.g., critical register contents) and 
reestablish the context when the interrupt occurs. Part of the context is automatically established by 
the processor: the device address and status, and (for auto driver channel operation) the CCB 
address is loaded into registers. Any other values required must be loaded by the interrupt service 
routine (ISR). 

Interrupts may be serviced by ISRs by the auto driver channel. Immediate ISRs, entered directly 
from an ISPT vector, are not used frequently in OS/32 device drivers. Rather, all interrupt service 
is via the auto driver channel, even if only to pass control to the ISR (no execute mode). The reason 
for this is that the auto driver channel supplies the address of the CCB in register 4. This allows the 
operating system, by software convention, to extend the CCB to contain device specific state data 
and/or pointers to other structures managed by the I/O subsystem. 

The following sections give examples of both immediate service and Auto Driver Channel 
operation. It will be noted that the immediate interrupt example, i.e, setup and service, is a model 
for Auto Driver Channel setup and interrupt service. The only difference between immediate ISRs 
and auto driver channel ISRs is the CCB addresses in register 4 supplied by the channel. 
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3.2.2.1 Immediate Interrupt Service 

Immediate Interrupt programming, like all interrupt programming, consists of three phases: 
initialization, interrupt service and termination. Initialization involves initializing appropriate I/O 
data structures (specifically the ISPT) and preparing the device. 

Interrupt service is handled by a routine whose address is placed in the ISPT by the initialization 
phase. Termination includes all processing after the interrupt phase has encountered a termination 
condition (all data transferred, device error, I/O halted). In OS/32, the termination phase must be 
scheduled by adding a structure to the system queue. This will be discussed further in the following 
chapters on the OS/32 I/O subsystem and device driver structures. The following is an example of 
an initialization and interrupt service phase using an immediate ISR. For the initialization phase, 
assume that the memory locations named CURBUFAD and ENDBUFAD, contain the start and 
end address, respectively, of a data input buffer. Further, assume that register R6 contains the 
device address. The ISPT and device might be set up as follows: 



LA RO,ISRODEVR Address of device ISR 

STH RO,ISPT(R6,R6) Set ISR for interrupt 

OC R6,SETUPDEV Command device - enable interrupts 

B WAITTERM Wait for termination 



The STH instruction places the ISR address into the ISPT at offset of twice the device address. On a 
3200 IOP, the ISR address would be stored at a fullword offset (4 times the device address). A 
slightly different sequence of instructions must be used if the device driver must support devices 
under both the CPU and IOP. See Chapter 8 for more information concerning differences for 
writing a driver under an IOP. The OC instruction sends the command byte at location 
SETUPCMD that, presumably, enables interrupts. This example then branches off to WAITTERM, 
to wait for the interrupt service phase to schedule the termination phase. 

The ISR is entered when the device requests attention. The following ISR reads a byte of data from 
the device into the buffer until the buffer is full: 
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PURE 




ISRODEVR 


THI' 


E3,STATMASK 




BNZ 


ISROEXA 




THI 


E3,STAT.BSY 




BNZ 


ISROEXIT 




L 


E6,CURBUFAD 




RD 


E2,0(E6) 




AIS 


E6,l 




ST 


E6,CURBUFAD 




CL 


E6,ENDBUFAD 




BP 


ISRTERM 


ISROEXIT 


LPSWR 


EO 



Test for error status 
Examine status 
Device just busy? 
Yes, ignore interrupt 

Current buffer address 

Read data into buffer 

Increment. . . 

and store updated buffer address 

Check if buffer full 

Schedule termination 

Exit ISR 



This ISR is entered on a device interrupt with registers EO through E3 initialized by the processor's 
microcode. Note that registers are referred to by mnemonics beginning with an "E." This is to to 
indicate that the ISR is executing in one of the Executive register sets. 

Register E3 contains the device status, that the example ISR tests for interesting status (defined by 
symbol STATMASK) and for device busy. Error conditions will be handled by code off at label 
ISROEXA. If the device is still busy, the example exits by branching to ISROEXIT. This test may 
be necessary for some devices to ignore any spurious interrupts that might be queued when the 
device interrupts are enabled. 

The next section of the ISR reads a byte of data from the device (address in E2, thanks to 
microcode) into memory at the current buffer location. The buffer address is incremented and 
compared to the end address. If the update buffer address is greater than the end address, 
termination phase is scheduled at ISRTERM (not shown). Otherwise, the ISR exits at ISROEXIT. 

The ISR exits by loading the old PSW and LOC placed in registers EO and El by the microcode. 

3.2.2.2 Auto Driver Channel Programming 

The auto driver channel is a set of microcoded ISRs provided in the basic control store of the Series 
3200 Processors. It can be controlled via a CCB to perform very simple or fairly complex I/O 
transfers. Each interrupt can be handled entirely within microcode until an error or normal 
termination condition forces entry into a channel ISR. 
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On the other hand, the channel operation can be completely bypassed. By resetting the Channel 
Control Word (CCW) Execute bit (CCWEX), all interrupts are passed directly to the ISR. This is 
called the no-execute mode. In this mode, the data transfer in the immediate interrupt example (in 
the preceding section) could be initialized as follows: 



LA RCCCBDEV 

LIS 110,0 

STH RO,CCB.CCW(RC) 

LA RO,ISRODEVR 

STH RO,CCB.SUBA(RC) 

AIS RC,1 

STH RC,ISPT(R6,R6) 

OC R6 , SETUPCMD 



Address of CCB 

Set no -execute CCW 

Address of ISRO 

Set ISR in CCB 

Address of CCB+1 

Set CCB address in ISPT 

Set up device - enable interrupts 



This initialization routine set up only the CCW and the ISR address (SUBA) in the CCB. The 
address+1 of the CCB is stored in the ISPT and device interrupts are enabled. The same ISR as the 
immediate ISR example can be used to service this I/O. All interrupts will be passed directly to the 
ISR. The only difference is that, on each interrupt, register E4 will be preloaded with the address of 
the CCB. This might be useful, for example, to the routine that schedules termination. Also, the 
ISR could be improved to use buffer addresses with the CCB, rather than global symbols. 

This first example illustrates how the auto driver channel can be used together with immediate ISRs 
simply to get the CCB address. The following example uses the auto driver channel in the fast 
mode to transfer a buffer of data from the device to memory. Assume the following register 
contents: Rl and R3 contain the buffer start and end addresses, respectively; R6 contains the device 
address and RC contains the CCB address: 
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LI RO,CCWSTAT+CCWEX+CCWFST 



STH 


RO,CCB.CCW(RC) 


ST 


R3,CCW.EBO(RC) 


SR 


R1,R3 


STH 


Rl,CCW.LBO(RC) 


LA 


R0,ISR1DEVR . 


STH 


RO,CCB.SUBA(RC) 


AIS 


RC,1 


STH 


RC,ISPT(R6,R6) 


OC 


R6 , SETUPCMD 



Set CCW= EXEC (READ) FAST 
Set buffer to end 
Calculate negative length 
Set length in CCB 

Set ISR address 

CCB address+1 

Set CCB address in ISPT 

Set up device-enable interrupts 



In addition to the CCW and ISR fields, the CCB buffer parameters are initialized. The ISPT is 
then set up with the CCB address+1, and device interrupts are enabled. 

As bytes of data arrive at the controller, busy drops and the device interrupts the processor. The 
auto driver channel receives control (as for the first example) because the ISPT entry is odd. The 
CCW specifies Execute, (Read) and Fast. 

The channel fetches the device status and tests it against the CCW status mask. If any error bits are 
set, the ISR is entered with a condition code (<0) set. If no error status is raised, the channel 
accesses the buffer length field (LBO). If LBO is positive, the ISR is entered with a condition code 
(>0) set. If LBO is nonpositive, it is added to the end of buffer (EBO) to yield the current buffer 
address. 

A data byte is read from the device and placed in memory at the current buffer address. The buffer 
length field is then incremented. The processor exits from the channel to continue processing 
suspended when the interrupt occurred. From the discussion above, it should be clear that the 
channel has handled the entire buffer read operation. The ISR is only entered to handle device 
errors and buffer full (i.e., channel termination). Aside from the actual error handling and 
termination code, the ISR is quite simple: 
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ISRDEVR BM ISR1ERR Device error 

BP ISRTERM Schedule termination 
LPSWR EO Ignore others 



The ISR branches directly on the condition code set by the channel. It should never (in this 
example) fall through to the LPSWR instruction, unless the CCW execute bit were explicitly reset. 

More complex operations can be handled by the auto driver channel. For example, the initialization 
phase could be set up by CCB Buffer 1 parameters (LB1.EB1) in addition to buffer 0, and could 
reset the CCW fast bit. Then, when buffer became full, the channel would automatically switch to 
bufferl by complementing the CCW buffer switch bit. At the same time the ISR is entered with a 
buffer full condition code. 

By initializing the CCB check word field and selecting a redundancy checkword generation in the 
CCW, the channel can accumulate a check sum for the transfer. Finally, character set translation 
and special character trapping can be handled by setting up a translate table and enabling translation 
in the CCW. 

3.3 DIRECT MEMORY ACCESS (DMA) PROGRAMMING 

DMA programming transfers data directly between device and memory using the DMA channel. 
The DMA channel for Perkin-Elmer Series 3200 is called the Selector Channel (SELCH). DMA 
programming involves programming the SELCH to perform the data transfer, as well as setting up 
the device. Interrupt programming is used to service the SELCH terminations (errors or end of 
buffer). 

3.3.1 The Selector Channel (SELCH) 

The SELCH controls the data transfer between high speed peripheral devices and memory, without 
processor intervention. A SELCH can be connected to a maximum of 16 devices. The SELCH is a 
half-duplex, block transfer channel. It can transfer data between memory and a single selected 
device. Hence, the name selector channel. The advantage of using a SELCH is that, once 
initialized, the SELCH is completely self-supporting, and the processor is free to perform other 
tasks. 

The SELCH is programmed via the multiplexor (MUX) bus and via the MUX bus, it supplies the 
status of the transfer. Both the SELCH and the device controllers, which are connected to it, have 
individual device addresses on the MUX bus. 
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The SELCH has two registers in which the current address and the end address of the data transfer 
will be stored. The starting address of the data transfer is the first current address. This must be 
done before the SELCH is started. Using a WRITE instruction, the device driver stores this 
information into these registers. 

During the actual data transfer, the SELCH will automatically update the current address register, 
until it is equal to the end address. This indicates the end of the transfer and cause the SELCH to 
stop. 

During the operation, the SELCH collects the data bytes or halfwords from the peripheral and 
transfers halfwords to memory. For this reason the start address must be on a halfword boundary 
and the end address must be odd. 

After the SELCH has stopped, the controlling program should verify that the current address 
register contains the end address of the buffer. If this is not the case and if they were properly 
programmed, a device malfunction or an exceptional situation has occurred. For example, a disk 
cylinder was exhausted and the transfer had to be interrupted to enable repositioning of the heads. 
Depending upon the device, more information can be obtained by examining the status of the device 
or the SELCH. 

There are two SELCH modes, the idle mode and the run mode. In idle mode, the private 
multiplexor bus (PMUX) is connected to the MUX bus. The SELCH generates its own PMUX to 
which device controllers such as disk and tape are connected. In the idle mode, the connected 
PMUX allows the CPU to address device controllers to set up for transfers. In the run mode, (i.e, 
the SELCH is monitoring the device and transferring data) the PMUX is disconnected from the 
MUX. The CPU is unable to access device controllers on the PMUX. The SELCH monitors the 
last device accessed, the selected device on the PMUX. 

Drivers must always explicitly kill the SELCH via the output command before attempting to access 
devices under SELCH. 

3.3.2 Programming the Selector Channel (SELCH) 

The usual method of programming with the SELCH is the immediate interrupt. The first step in the 
operation is to check the status of the SELCH. If the SELCH is not busy, the address of the 
termination ISR is placed in the location in the ISPT for the SELCH device number. The program 
should then proceed as follows: 

1. Give the SELCH a command to stop (i.e., kill the SELCH). This command initializes the 
SELCH registers and assures the idle condition of the PMUX connected to the I/O bus, so that 
the device may be set up for data transfer. 

2. Write the buffer start and end addresses to the SELCH. 

3. Prepare the device for the data transfer with the required commands. 

4. Give the SELCH the command to start (READ or WRITE). 
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With the start command, the SELCH breaks the connection between its PMUX and the processor's 
I/O bus, and provides a direct path between memory and the last device addressed over its bus. 
When the device becomes ready, the channel starts the transfer, which proceeds to completion 
without further processor intervention. Once the start command has been given, the processor can 
proceed to the execution of concurrent instructions. 

It is imporant to note that the driver must not be interrupted between Steps 3 and 4 described above. 
The reason for this is as follows: 

• Step 3 causes the device to be selected on the PMUX bus. It should be left selected by being the 
last addressed device in Step 3. 

• Step 4 causes the SELCH to do a status loop I/O transfer between memory and the selected 
device on its PMUX bus. The SELCH has no device address generation capability on the PMUX 
so that it selects the last device addressed by the CPU in Step 3. 

• If an interrupt were to occur between Steps 3 and 4, the interrupting device would be selected 
and the device selected in Step 3 would be deselected. When the SELCH is started in Step 4, it 
would attempt to transfer to or from the wrong device. 

Drivers should disable interrupts at all priorities by setting program status word (PSW) bits 17 and 
20 to zero. This is true even within ISRs. 

Upon termination, the SELCH signals to the processor that it requires service. The processor 
subsequently takes an immediate interrupt, transferring control to the SELCH ISR. At this time, 
registers to 3 of the new register set are set as for any other immediate interrupt. 
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CHAPTER 4 
THE INPUT/OUTPUT (I/O) SUBSYSTEM ARCHITECTURE 



4.1 INTRODUCTION 

This chapter describes supervisor calll (SVC1) instructions and connect/disconnect queues. It also 
gives a description of data structures connected with I/O subsystems. 

4.2 SUPERVISOR CALL1 (SVC1) SYNOPSIS 

The SVC1 internal interrupt handle is responsible for servicing task I/O requests. SVC1 runs as in 
the nonreentrant system state. That means that it executes in register set with system queue 
service (SQS) interrupts disabled, nonreentrant system state routines are restricted to registers 8 
through 15 of set 0. 

An I/O request is encoded in an SVC1 parameter block described in the following section. The 
parameter block indicates the I/O function requested and contains a task-specific logical unit (lu) 
number indicating on which device (or file) the request is to be performed. The remainder of the 
parameter block contains additional arguments for the request and space for returned status and 
other information. SVC 1 has major functions which it performs. They are the following: 

. Validation of the specified logical unit: is it within the task's range of valid logical units? Is it 
assigned to a device? 

• Validation of the data buffer start and end addresses if the request involves data transfer. 

• Acquisition and initialization of an Input/Output Block (IOB) if the request requires activation of 
the device driver. 

. Validation that the request is legal for (i.e., supported by) the device. 

• Invocation of a (possible device-specific) I/O handler (IOH) - a routine which performs or 
schedules the device driver to perform the I/O request. 

All VO requests are directed to an lu. Each task has from 1 to 255 logical units. An lu may be 
assigned to a device or file. If an lu is assigned to a device, the entry for that lu in the task's lu table 
contains a pointer to a data structure called a device control block (DCB). For a file, the lu table 
entry is the address of a file control block (FCB), which is very similar to a DCB. This manual is 
primarily concerned with device drivers. 

Not all I/O requests actually perform data transfer. Some are command functions (e.g., REWIND), 
which access the device via the driver, but do not require a data buffer. Some requests do not even 
require entry into the driver - they are executed completely by the I/O supervisor. Examples of such 
requests are Wait Only, Test I/O Complete or Halt I/O. 

Requests that require activation of the device driver are copied into a data structure called an IOB. 
IOB's are used to queue multiple I/O requests to devices that might be busy with a prior request. 
IOBs are discussed in Section 4.3.3. 
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SVC1 must validate that the requested function is legal for the device as currently assigned. That is, 
does the device support the requested function and does its current access privileges (e.g., 
Read/Write, Read Only, Write Only) permit the requested function. The Read/Write validation is 
performed explicitly by testing the function request against device attributes as modified by Access 
Privileges. These modified attributes are stored as part of the lu entry in the task's lu table. 
Validation of other functions (e.g., Rewind, Halt I/O, etc.) is performed implicitly when the I/O 
Handler is invoked. 

The I/O supervisor is sometimes called the SVC1 skeleton. This is because it performs all of the 
actual I/O request processing, once all of the required validations have been performed, by calling a 
(possibly device-specific) IOH. The I/O handlers for a device driver are contained in a table called 
the IOH list. The IOH list is located by a pointer field in the DCB. Thus, each device type can have 
its own device-specific IOH. The IOH list contains one entry for each I/O request function (plus 
entries for system functions such as system initialization or power restore). For each supported 
function, the IOH list entry is the address of the SVC1 executor for that function. Entries for 
unsupported functions point to the SVC1 illegal function handler (SVC1FCER). The IOH list is 
described in Chapter 5. 

After performing the requested function or scheduling the device driver to perform the request, 
SVC1 exits via the task dispatcher to continue task processing. See Table 4-1 for an illustration of 
the SVC1 parameter block. 
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TABLE 4-1. SVC1 PARAMETER BLOCK FORMAT AND CODING 



0(0) 
Function code 


1(1) 
lu 


2(2) Device- 
independent 
status 


3(3) Device- 
dependent 
status 


4(4) 




Buffer start address 


8(8) 




Buffer end address 


12(C) 




Random address 


16(10) 




Length of data transfer 


20(14) 




Extended options 



SVC 



l,parblk 



ALIGN 4 








parblk 


DB 


X ' function code ' 






DB 


X'lu' 






DS 


2 bytes for status 






DC 


A (buffer start) 






DC 


A (bu f f er end) 






DC 


4 bytes for random 


address 




DS 


4 bytes for length 


of data transfer 




DC 


Y' extended options 





Where: 



• The function code is a 1-byte field indicating whether a request is a data transfer or a 
command function, and the specific operation to be performed. 

• lu is a 1-byte field containing the lu currently assigned to the device to which an I/O request is 
directed. 

• Device-independent status is a 1-byte field receiving the execution status of an I/O request 
after completion. The status received is not directly related to the type of data used. 

• Device-dependent status is a 1-byte field receiving the execution status of an I/O request after 
completion. The status received contains information unique to the type of device used. 
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• Buffer start address is a 4-byte field used only for data transfer requests and must contain the 
starting address of the I/O buffer that receives or sends the data being transferred. 

• Buffer end address is a 4-byte field used only for data transfer requests and must contain the 
ending address of the I/O buffer that receives or sends the data being transferred. 

• Random address is a 4-byte field containing the address of the logical record to be accessed for 
a data transfer request; a legal binary number must be specified in this field if bit 5 of the 
function code is set to 1. 

• Length of data transfer is a 4-byte field used only for data transfer requests. It receives the 
number of bytes actually transferred as a result of a data transfer request. If an error occurs 
during data transfer, this field is modified with indeterminate data. 

• Extended options is a 4-byte field specifying device-dependent and device-independent 
extended functions that must be executed by the device when it is servicing a data transfer 
request. 

4.2.1 Description of Special Supervisor Call 1 (SVC1) Functions 

The following section gives a brief description of various special SVC1 functions. 

4.2.1.1 Command/Data Transfer 

Command/data transfer is bit of the SVC1 function code (SVC1.CMDF) and determines whether 
the request is a data transfer (READ or WRITE) or command request. When SV1.CMDF is set 
(1), the function is a command request. Otherwise, it is a data transfer request. 

4.2.1.2 Read/Write 

Bit 1 of the function code is the read (SV1.READ) bit. Bit 2 is the write (SV1.WRIT) bit. If both 
are set, the function is formally a TEST2SET used to READ-MODIFY-WRITE a lock bit in a file 
record/data block. A driver can interpret this code as anything it desires, e.g., "read after write." 

4.2.1.3 Wait Read/Write 

When the function code wait bit (bit 4) is set, the calling task will be placed in an I/O wait state 
until the request has been completed. When the wait bit is reset, the request is a proceed request. 

4.2.1.4 Proceed Read/Write 

If the device is not in use, this function causes an I/O request to be initiated and control returned to 
the calling task immediately. If the device is busy, the request is enqueued unless an unconditional 
proceed is requested. Control is then returned to the calling task. When the total number of 
enqueued I/O requests exceeds the maximum number of IOBs established at link time, the calling 
task is placed in an IOB wait state. The task is awakened when one of its enqueued requests gains 
the connection and an IOB is released. 
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4.2.1.5 Unconditional Proceed Read/Write 

This function behaves in exactly the same manner as the PROCEED READ/WRITE function, 
except when the maximum number of enqueued I/O requests are reached. Exactly n requests can be 
enqueued at any moment in time. 

The condition code is set to when the request gains the connection or when it is successfully 
enqueued. When the maximum number is exceeded, the request would not be enqueued. In this 
case, the error status is set to X'F'. A condition code X'O' implies either the request gains the 
connection or is successfully enqueued. 

4.2.1.8 Wait-Only 

This function is interpreted as a wait for the completion of all pending I/O requests to the specified 
lu of the calling task. A pending I/O request implies either an ongoing I/O or an enqueued request. 

4.2.1.7 Test Input/Output (I/O) Completion 

This function returns a condition code of X'F' if any request is pending on the specified lu of the 
calling task. If not, the condition code is X'O'. 

4.2.1.8 Halt Input/Output (I/O) 

This function aborts all outstanding requests issued to the specified lu of the calling task. 

4.2.1.9 Test and Set 

The test and set function provides a synchronization mechanism for concurrent accesses on the same 
file by different tasks. It allows a task to access a record within a file and, at the same time, mark it 
as being in use. The first bit in the record is reserved for this purpose. If it contains a 0, the record 
is not currently in use. If it contains a 1, the record is by convention in use. Readers interested in 
specific details are referred to OS/32 MTM Programming Reference Manual. This function is 
implemented within all disk drivers and is therefore supported both for contiguous and indexed files 
as well as bare disk accesses. 

4.3 THE DEVICE CONTROL BLOCK (DCB) 

For every device specified there is a DCB. The DCB is the data representation of a logical device 
within the OS/32 I/O subsystem. A file control block (FCB), which is a variant of a DCB, 
represents a file and is a type of logical device. Tasks open devices (or files) by placing the address 
of the DCB (or FCB) in the task's lu table (along with the read/write access privileges granted). A 
DCB consists of two parts: 

• The device-independent part of the DCB is defined by the I/O Subsystem Architecture. It 
contains fields used by SVC1 and SQS, to schedule the driver and to communicate parameters 
and status between the driver, the OS and the task. 

• The device-dependent part of the DCB is defined by the device driver. It contains internal driver 
state information, and possibly, trace/debug information. 
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The field's layout for the device-independent DCB and for the standard device-dependent DCB is 
given in Appendix A. 

The device-independent part of the DCB is analagous to a task's task control block (TCB). It is the 
per device system data structure. As such, it contains data of interest to SVC1 and SQS, for 
example: 

• the address of the physical device's event coordination leaf (see Section 4.S), 

• the address of the IOH (discussed in Chapter 5) for this device, 

• I/O request queueing strategy routine address should this device require special request 
queueing, 

• driver initialization entry points for data transfer and command requests and the driver 
termination entry point, 

• the optional address of a special I/O completion handler, 

• device time-out chain link field and time-out value 

• an embedded IOB (see Section 4.3.3) containing the "connected" I/O request, if any. 

There are other fields in the DCB used by SVC1 for systems that contain Series 3200 I/O Processors 
(IOPs). These fields contain the IOP number to which the address is attached (0 for the CPU) and 
the address of the system queue for this device. 

The device-dependent part of the DCB is analogous to a task's impure data area. All device drivers 
are written to be re-entrant (so that there need be only one copy of the driver for many devices). 
Thus, the driver stores all state information and possibly, debug or trace data in the device- 
dependent DCB. 

A detailed description of the DCB can be found in Appendix A. 

4.3.1 The Device Mnemonic Table 

All devices and device volumes with direct access are specified in the system and by the user 
programs, either by showing a logical device number, or by showing a unique 4-character 
mnemonic. In order to relate this mnemonic to a device, the system uses a list of these devices, 
together with the device's DCB. The Device Mnemonic Table lists the relation between device 
mnemonic and the address of its DCB. 
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TABLE 4-2. DEVICE/VOLUME MNEMONIC TABLE 



DEVICE MNEMONIC TABLE 



DEVICE MNEMONIC (ASCII) 
ADDRESS OF RELATED DCB 



DEVICE MNEMONIC (ASCII) 



ADDRESS OF RELATED DCB 



DEVICE MNEMONIC (ASCII) 



ADDRESS OF RELATED DCB 



Y '00000000' 



Y '00000000' 



Figure 4-1 shows relationships of system pointer table (SPT), device mnemonic table (DMT), 
volume mnemonic table (VMT) and DCBs. 

NOTE 

The SPT, DMT, and VMT are normally not referenced by 
I/O drivers. 
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SPT.DMT 



SPT.VMT 



SPT 



VOL1 



A(DMT) 



VOL2 



A(DMT) 



VMT 



DCB.DMT 




MNEM1 



A(DCB) 



MNEM2 



A(DCB) 



MNEM3 



A(DCB) 



DCB 




DCB.DMT 



DCB 



DMT 



DCB.DMT 



DCB 



Figure 4-1. Device and Volume Mnemonic Tables Address Linking of DCBs 

4.3.2 Device-Independent Status Values 

Logical units provide device-independent I/O by causing all I/O requests to be made directly to the 
lu and not to the device. The execution status of an I/O request that is independent of the physical 
characteristics of the device being used is returned to the device-independent status field of the 
parameter block (see Table 4-3). The data remaining in this field from a previous I/O request is not 
modified until a subsequent I/O is completed or an error occurs. 
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TABLE 4-3. DEVICE-INDEPENDENT STATUS CODES 



STATUS 
CODE 


MEANING 


X'CO' 


Illegal function - an error is present in the function 
code; the requested function is not supported by the device 
or assigned access privilege or the buffer transfer is too 
small. When using tape, minimum buffer size is four bytes. 


X'AO' 


Device unavailable - the device is either inoperative or 
not configured into the system . 


X«90' 


End of medium (EOM) - The I/O directed to the lu reached 
the physical end of the device, e.g., end of tape. During 
magnetic tape operations, this status can be combined 
one of the next three status codes, yielding X'98', X'94', 
and X'92\ 


X'88' 


End of file (EOF) - the logical end of file specified by 
the assigned lu was reached. 


X'84' 


Parity - an even or odd parity error occurred on a 
data transfer request. 

Recoverable error - the I/O request is recoverable 
and can be retried. A write request was issued to a 
write-protected device. 

No I/O currently being processed - if a halt I/O is requested 
is executed, this bit is set, indicating that no I/O is being 
processed at this time. 


X'81* 


Illegal or unassigned lu - the lu specified in the parameter 
block is either incorrect or was not previously assigned. 


X'OO' 


Normal execution or successful I/O is completed, and 
no error occurred. 



The origin of the status, i.e., whether it came from SVC1 or the driver, varies: 

X'CO' Originates from SVC1 if attributes do not match function (READ/WRITE), or if IOH 
list does not have entry for the function. 
Originates possibly from driver itself after further checks (e.g., buffer alignment). 

X'AO' Originates from the driver either because false sync received (no such device) or device 
status indicates off-line/powered down. 
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xw 



Originates from driver. 



X'88' Originates from driver. 

X'84' Originates from driver. 

X*82' Originates from driver or from SVC1 (e.g., for halted queued I/O requests.) 

X'81" Originates from SVC1 if lu illegal or unassigned. 

There are several instances where the device-dependent status field contains what is actually device- 
independent status. This is always used in conjunction with device-independent status X'82\ The 
possible status codes are given in Table 4-4. 

For example, when a device times out, the driver, by convention, usually returns status X'8282'. A 
driver might return a different value if, for example, there are several possible time-out conditions 
which the driver wants to signal (e.g., time-out waiting for seek complete, time-out during data 
transfer, time-out waiting for protocol ACK, etc.). Another example is when an I/O is halted. The 
driver normally returns status X'8281' (as shown in Table 4-4). 



TABLE 4-4. DEVICE-DEPENDENT STATUS CODES 



STATUS 
CODE 


MEANING 


X'85' 


Exhausted retries on seeks - seeks on disk devices 
have been retried the maximum number of times. 


X'84' 


Queued I/O terminated - a queued I/O request is terminated 
because a previous I/O request failed. 


X'83' 


Device is write-protected - a write operation to a 
write-protected device occurred. 


X'82' 


Read/write time-out - a read or write time-out condition 
occurred. 


X'OO* 


Normal execution - I/O was completed and no error occurred. 



4.3.3 The Input/Output Block (IOB) 

The (IOB) is a data structure that represents an I/O request within the I/O subsystem. An IOB is 
only required for those requests that will involve the device driver in accessing the device. It 
contains all of the information required by the I/O subsystem to queue and process the request. This 
information includes: 



4-10 



48-190 F00 R00 



• A copy of the SVC1 parameter block, 

• Both the unrelocated (physical) and relocated addresses of the SVC1 parameter block. The latter 
is used in forming the task Q entry for proceed I/O requests. 

• The address of the TCB of the task requesting the I/O. 

• The address of the DCB for the device. 

• The driver entry point to be used when a device event is scheduled for this request. 

• Request dependent flags that specify various optional processing for this request. 

• Link fields for queueing the I/O request. 

IOBs are maintained in a free pool for each task. The number of IOBs a task will have is specified 
when the task is linked. The default is one in order to ensure that every task has at least one IOB. 
IOBs are allocated within system space at task load time. 

SVC1 gets an IOB from the requesting task's free pool by calling the routine GETIOB. IOBs are 
released to the free pool by calling RELIOB after the request is connected to the device (leaf), and 
the contents of the IOB have been copied into the DCB's embedded IOB. If it is necessary to queue 
the request and if the request resides in the task's last or only IOB, the task is placed in "IOB 
Wait." It cannot proceed (i.e., exit from SVC1) until at least one queued request has been connected 
and the IOB released. Because of this convention, GETIOB will always find at least one IOB in the 
free pool when called from SVC1 . 

The IOB event service routine (ESR) field is initialized by SVC1 to contain one of the two driver 
initialization routine entry points (for data transfer or command functions). This field governs the 
entry to the initialization phase of the driver when the IOB is copied into the DCB's embedded IOB 
at connection time. This same field in the embedded IOB is modified by routines EVMOD or 
DIRDONE to contain the address of intermediate or termination ESRs. 

The "request dependent flags" field is used to specify which optional processing of the request is to 
be performed. This includes: 

• removing IOB wait on device connection, 

• removing I/O wait or adding a parameter to task Q on I/O completion, 

• overriding reset of Interrupt Service Pointer Table entry on I/O completion, and others. 
A detailed description of the elements in the IOB can be found in Appendix A. 

4.3.4 SUPERVISOR CALL 1 (SVC1) Exits 

Except for memory faults, SVC1 exits to the task dispatcher when it has completed IOH processing. 
As a result of the IOH, the disposition of the request will be one of the following: 

• connected to the device and driver initialization scheduled, 

• queued to the device, controller or selector channel (SELCH), 
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• aborted because of an error, or 

• completed within the IOH routine. 

Depending on the disposition of the request, different post-processing will be required, including: 

• releasing an IOB if one was gotten and it has not been queued, 

• placing the task in IOB or I/O wait, if necessary, and 

• adding a trap item to the task queue. 

Several different exit routines are provided to perform this post-processing. These routines are made 
entry points so that custom I/O can use them. Most of the standard IOHs exit to one of these 
routines. Some IOH exit directly to the task dispatcher. 

4.3.4.1 Normal Exits 

The following exit routines are normal (nonerror) exits or common routines used for both normal 
and error exits: 

• SVC1EXIT - normal exit for driver requests (data transfer or commands). This routine sets 
IOB or I/O wait as appropriate and remembers in the IOB flags (in the DCB's embedded IOB) 
whether to move I/O wait or add an I/O completion trap to the task's queue. It exits to the task 
dispatcher. 

• SVCINOOP - IOH exit to ignore the function (i.e, no operation). This routine is normally 
referenced directly from the IOH list for functions that are to be ignored. It returns a zero status 
to the SVC1 parameter block and exits to one of the following common exit routines. 

. SVC1NINA - (No IOB, no ADD to task queue) exits directly to the task dispatcher. 

• SVC1INA - (IOB, no ADD to task queue) adds task trap item (I/O completion reason code plus 
SVC1 parameter block address) to the task's queue, then exits via SVC1NINA. 

• SVC1IA - (Both IOB and ADD to task queue) releases IOB and exits via SVC1NIA to add to 
the task queue. 

4.3.4.2 Error Exits 

The SVC1 error exits are: 

1. SVC1FCER - Illegal Function Code. An illegal function code status (SV1E.IFC = X'COOO') is 
returned to the task's SVC1 parameter block. This routine exits to one of the SVC1 (N)I(N)A 
routines depending on whether an IOB needs to be released or a task queue trap is required. 

2. SVC1ADER - Address error. This routine exits to MEMFAULT, the memory fault 
(alignment, write protected, not present). 

4.4 SYSTEM QUEUE SERVICE (SQS) 

The SQS internal interrupt handler is the front door into the operating system for all external events 
such as I/O completions, timer events, and system power restore. Such events are signaled by 
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adding an entry to the system queue. 

The system queue entries are the addresses of device structures called leaves. For I/O events, the 
leaves are part of the eVent coordination tree discussed in Section 4.5. For other events such as 
timer events and and power restore, special leaves are created solely for the purpose of entering the 
SQS or event service state. These special leaves, which are not really part of the I/O subsystem, are 
described in Section 4.5.1. 

Each leaf contains the address of an SQS executor in the field EVN.SQS. After removing a leaf 
address from the system queue, SQS fetches and branches to the address of the SQS executor 
contained in the leaf. For I/O events, one of two executors (SQS.SLV or SQS.MLV) is invoked. 
These executors are described in Section 4.5.3. 

Ultimately, the SQS executor will enter a device driver in one of three event service routine (ESR) 
states: 

1. The driver initialization ESR to initiate a device operation. There are two possible 
initialization ESRs for drivers: one for data transfers (DCB.INIT) and command functions 
(DCB.FUNC). This ESR is scheduled by SVC1 if the device is not busy, or by the IODONE 
handler of a prior I/O. 

2. An intermediate ESR, such as a seek, complete on a disk. This ESR is scheduled by a device 
interrupt service routine (ISR). The actual ESR entry point is selected by a driver by calling 
the routine EVMOD. 

3. The driver termination ESR. This ESR is scheduled by a device ISR, or possibly, the system 
timeout routine. The termination ESR (DCB.TERM) is automatically selected when the 
Initialization ESR exits via DIRDONE (see Section 4.5.5). 

4.5 The Event Tree (EVT) 

The event tree is a tree-like structure built out of the combination of device leaves and controller, 
SELCH and EDMA nodes. The tree mirrors the hardware configuration of the system (selector 
channel, device control, devices). The tree is inverted with its leaves at the bottom and its root at 
the top. The tree is always processed upwards from the leaf. All of the resources necessary to 
perform I/O, such as a SELCH or controller, shared by more than one device, must be acquired for 
use by a driver. The EVT handles the allocation of these shared resources. Figure 4-2 gives a 
detailed description of the event coordination tree. Note the following in reference to Figure 4-2: 

EVN.DCB = ==> LEAF /NODE free. 

EVN.DCB = A(DCB) ==> LEAF /NODE connected. 

When LEAF is connected, DCB.IOB contains IOB of current I/O. 
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Figure 4-2. The Event Coordination Tree 



For example, an I/O request for a disk device starts at the IOB, then passes to the leaf, the disk 
controller node, the SELCH node and possibly to the optional EDMA or super node. The structure 
of each leaf (lowest node) or other node is discussed in Appendix A. 

It is important to note that the event coordinating structure contains two waiting queues, one for 
leaves and another for IOBs. IOBs are queued to leaves, thus representing I/O requests to a busy 
device. Leaves and nodes are queued to higher level nodes if the node is busy servicing another 
request. 

Figure 4-3 depicts the queueing of I/O requests to a device. The structures depicted in Figure 4-3 
are controlled by the operating system I/O executive routines. They are not accessed by I/O drivers. 
Figure 4-4 depicts the queueing of I/O requests to a disk device. 
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Figure 4-3. Queneing of I/O Requests to a Device 
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Figure 4-4. Qneneing of I/O Requests to a Disk Device 



4.5.1 Resource Nodes 

Resource nodes are created at system generation (sysgen) time, and represent logical resouces 
rather then devices. 

DIRECTORY LEAF and BIT MAP LEAF are noneventing. They behave like locks on the 
directory or bit map resource. These leaves are not the concern of the Series 3200 I/O subsystem. 
Other leaves (TIMER, POWER RESTORE, TIMESLICE) are all eventing leaves. They are 
placed on the system queue to force entry into the SQS state. The EVN.SQS fields in the leaves 
contain special executors outside of the I/O subsystem . 

4.5.2 Extended Direct Memory Access (EDMA) Node 

The EDMA node is used to limit the number of concurrent data transfers on the DMA bus. This 
node, if required by hardware configuration, must be specified at sysgen time by the 
COORDINATION statement. The COORDINATION statement has parameters which describe 
the SELCHs or devices that are to be coordinated and an optional parameter to specify the 
maximum number of simultaneous transfers. 

4.5.3 System Queue Service (SQS) Executors 

The single level and multilevel device dispatchers are the SQS executors. 



4.5.3.1 Single Level Device Dispatch (SQS.SLV) 

This algorithm is designed for devices attached to the multiplexor (MUX) bus. A test for connection 
is simply a test of a parameter (connected DCB address) for zero. If the leaf is indeed connected, 
then the driver is entered at the current event service routine entry point, which is found in 
DCB.ESR. 

For disconnection, the DCB address in the leaf is zeroed. If the IOB queue is not empty, the top of 
the queue is selected for connection. Data from this IOB is then moved to the DCB. The DCB 
address in the node is updated and the leaf is added to the system queue so that the driver may be 
scheduled in its turn. The IOB is then released, and if the task was in an IOB wait, the wait is 
removed. 

4.5.3.2 Multilevel Device Dispatch (SQS.MLV) 

This algorithm is designed for devices attached to a shared controller and/or a SELCH. The current 
hardware I/O architecture requires the connection to the SELCH or controller before any 
communication is attempted to devices attached to it. This ensures that the channel or controller is 
not busy with another I/O. The connection algorithm starts from the first level device node (i.e., 
the leaf) and moves up each time a connection is successfully made. The request is always queued if 
the connection cannot be made. The connection algorithm at the first level device node is similar to 
simple device connection algorithm. For the connection at an upper level node, a test is made to a 
parameter (EVN.DCB) for zero. If zero, the requesting DCB address is saved and the connection 
is made. Otherwise, the requesting node is put on the tail of a first-in/first-out (FIFO) Q. For disks, 
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the default Q strategy will queue the node as the head of the queue last-in/first-out (LIFO) if a seek 
is required. This policy encourages overlapped seeks. 

If the connection is made up to the top of the tree, and the request is a non-data transfer request 
(for example, a seek), the driver ESR is entered (DCB.ESR). The complete connection is said to 
be made. For a data transfer request, and if an EDMA node has been configured, the EDMA node 
connection routine is called. If the request successfully connects to the EDMA node, the driver 
ESR is entered. 

The disconnection also starts from the bottom up. Each time a disconnection is made, the top of the 
waiting queue on that level becomes connected and enqueues to the next higher level node, if any. 

If the connection has been made to the EDMA node, the EDMA disconnection routine is called. If 
the queue at the at the top of the tree is not empty and the EDMA bus is needed, then the EDMA 
connection routine is entered. 

Some operations do not require the connection to all levels after the operation has been initiated. 
For example, a seek operation in general only requires connection to the disk. Therefore, the 
EVREL routine is supplied to release upper nodes. 

4.6 DRIVER SERVICE ROUTINES 

Two service routines are provided for drivers to control the sequence of ESRs to be executed and to 
control access to the event coordination tree. These are EVMOD and EVREL. 

4.6.1 EVMOD 

EVMOD is called by a driver initialization or intermediate ESR to select the next ESR to be run, 
i.e., when the device ISR adds the device leaf to the system queue or when the system "times out" 
the device. Normally, the driver termination ESR (DCB.TERM) is automatically selected when the 
DIR exits via DIRDONE. If the DIR made a prior call to EVMOD, the default selection is 
overridden. Thus, if a driver makes a call to EVMOD to select an Intermediate ESR, it must 
ultimately call EVMOD to explicitly select the termination ESR as it will not be selected by default 
thereafter. 

EVMOD is called as follows: 



L UF , DCB . LEAF (UD) 

LA UE,ESR_ADDR 
BAL U8 , EVMOD 

4.6.2 EVREL 

EVREL is called by drivers to release upper level nodes of the event coordination tree while waiting 
for some event which does not require those resources. The usual use is to release the SELCH and 
device controller nodes while waiting for a seek complete on a disk. 



48-190 F00 R00 4-19 



Note that when the event occurs and the device ISR schedules the event, it will be necessary for the 
device to reacquire these nodes before the ESR can be re-entered. This is the function of the 
SQS.MLV executor. EVREL is called as follows: 

L UF,DCB.LEAF(UD) 
LIS UE, level 
BAL U8, EVREL 

The level is the level in the event coordination tree at and above which the nodes are to be released. 
Level 2 will release both the controller and SELCH nodes. Level 3 will release just the SELCH 
node. 

4.7 DRIVER EXITS 

There are two basic types of driver exits: intermediate (nonterminal) exits and termination exits. 
The two intermediate exits, DIRDONE and EVRTE, are used when the current I/O request is not 
complete, but control is being returned to the operating system to wait for an external event. The 
termination exits, IODONE and IODONE2, are used when the I/O request is finished, either 
because of normal or error termination conditions. 

4.7.1 DIRDONE 

DIRDONE is the normal (nonerror) intermediate exit from the driver initialization. Its purpose is 
to set up DCB.ESR with the driver termination routine (from DCB.TERM), unless the driver has 
previously called EVMOD (see Section 4.6.1). DIRDONE exits to the SQS main exit, SQS.EX, 
which checks for more entries on the System Queue. 

4.7.2 EVRTE 

EVRTE is a normal exit from intermediate ESRs. It performs no function other than to exit directly 
to the SQS main exit, SQS.EX. 

4.7.3 IODONE 

IODONE is the main driver termination exit. It is called for all normal and error terminations with 
the resulting SVC1 status in DCB.STAT (2 bytes), and the length of transfer, if applicable, in 
DCB.LLXF (fullword). 

IODONE resets the HALT I/O Flag (DFLG.HIM) in the DCB.FLGS field and then checks for a 
device-specific IODONE handler in DCB.DONE. If one exists (DCB.DONE non-zero), IODONE 
branches to it. Such a device-specific routine may choose to return to IODONE after performing 
any device-specific processing. It may do so by branching back to the label IODCOM to perform the 
common processing described below. 

IODONE performs three main functions as part of its common post-processing of an I/O request: 

1. Return resulting status and length of transfer to the SVC1 parameter block via subroutine 
IODGST. 
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2. Remove I/O Wait or issue an I/O Completion Task Q trap for the task that requested the I/O 
via subroutine IODTWT. 

3. Disconnect the request from the event coordination tree and promote any queued IOB or nodes 
by invoking common disconnection routine (COMDIS). 

4.7-3.1 IODGST 

IODGST is called by IODONE to return the status (DCB.STAT) and the length of transfer 
(DCB.LLXF) to the SVC1 parameter block (DCB.PBLK). It may also be called by driver-specific 
I/O DONE handlers that choose not to return to IODCOM as discussed above. 

In addition to its primary functions described above, IODGST has one other function. It will reset 
the Interrupt Service Pointer Table for the device (DCB.DN) to ignore all interrupts (routine III). 
This function of IODGST can be overridden by setting IOBF.ISM in the request-dependent flags 
within the DCB's embedded IOB (DCB.RFLAG). Drivers that intend to service interrupts even 
when no request is active (e.g., terminal drivers that support "type-ahead") must be sure to set this 
flag. 

4.7.3.2 IODTWT 

IODTWT is called from IODONE or device-specific I/O DONE handlers to test the task trap and 
I/O Wait flags in the request dependent flags in the DCB's embedded IOB (IOB.RFLG). 

If the task trap flag (IOBF.TPM) is set, IODTWT will create an I/O completion task queue entry 
and enqueue it to the task queue of the task (IOB.TCB). If the I/O Wait flag is set (IOBF.IOM), 
then IODTWT will remove I/O Wait from the task. 

4.7.3.3 IODONE2 

IODONE2 is exactly the same as IODONE. It is maintained for compatibility with earlier revisions 
of OS/32. Prior to Revision 04 of OS/32, the driver initialization routine ran in a different state 
(RS-State) from the termination routines (ES-State). Therefore, driver initialization routines could 
not call IODONE. 

IODONE2 was provided as a termination exit for driver initialization routines - in thoses cases 
where the driver initial routine completed the request or encountered an error that required the 
request to be aborted. It is still common convention to use IODONE2 when it is necessary to 
terminate a I/O request from within the driver initialization routine. 

4.8 OTHER UTILITY ROUTINES 

4.8.1 Timer Services 

The OS/32 I/O Subsystem provides a timer with a resolution of one second for monitoring drivers 
which are waiting for external events. A driver utilizes the timer services by placing itself (i.e., its 
DCB) on the DCB time-out chain. This is accomplished by a call to the routine TOCHON (time- 
out chain ON), described below. 

Once a DCB is on the time-out chain, the action of the time with respect to that DCB is controlled 
by the halfword field DCB.TOUT. The possible values of DCB.TOUT and the corresponding time 
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actions are as follows: 

i DCB.TOUT = X'7FFF' - The timer is disabled. That is, the DCB will be ignored by the timer, 
even though it is on the time-out chain. Note: TOCHON initializes DCB.TOUT to this value. 

• 1 <= DCB.TOUT <= X'7FFE' - The timer is armed. Every second the system will examine 
each DCB on the time-out chain. If the value is between 1 and X'7FFE', inclusive, the timer 
logic will decrement DCB.TOUT by 1. If the value becomes zero, the device is timed-out. That 
is, an ESR is scheduled by adding the device leaf to appropriate system queue. It is the 
responsibility of all driver ESRs to check the value of DCB.TOUT for zero to recognize this 
time-out condition. 

• DCB.TOUT = zero - The device has already been timed-out (i.e., the timer ignores the DCB. 
All driver ISRs should check for DCB.TOUT = zero and exit immediately if that condition is 
found. Drivers should never schedule an ESR when DCB.TOUT = zero. 

• DCB.TOUT < zero - The timer is disarmed. That is, the driver has already scheduled an ESR. 
The timer will ignore the DCB. ISRs should also exit if DCB.TOUT < zero, so that a second 
ESR is not scheduled. 

It is not possible for a driver to tell when the one second timer event will occur. Therefore, to 
guarantee at least one second of time, the driver must always set DCB.TOUT a value greater than 
one when arming the timer. 

When a driver ESR detects a time-out (i.e., DCB.TOUT = zero), it should clean up, remove the 
DCB from the time-out chain (via a call to TOCHOFF), and terminate with a status of X'8282'. 

It should be noted that the Halt I/O function of SVC1 mimics a device time-out. That is, Halt I/O 
sets DCB.TOUT to zero and schedules the device ESR by adding the leaf address to the system 
queue. A Halt I/O is distinguishable from an actual time-out by the fact that a DCB flag 
(DFLG.HIM) is set in DCB.FLGS for a Halt. It is customary for a driver to terminate with a 
status of X'8281' when a Halt I/O is processed. 

4.8.1.1 TOCHON 

The subroutine TOCHON is called to place a DCB on the system time-out chain; normally from the 
Driver Initialization ESR. If the device is already on the Chain, the call is ignored. The call to 
TOCHON is coded as follows: 

BAL U8, TOCHON place DCB on time-out chain 

Register UD (13) must contain the DCB address, as it always does during driver ESR processing. 

4.8.1.2 TOCHOFF 

The subroutine TOCHOFF is called to remove a DCB from the system time-out chain. It should be 
called just before a driver exits to IODONE(2). If the DCB is not found on the time-out chain, the 
call is ignored. The call to TOCHOFF is coded as follows: 
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BAL U8,T0CH0FF 

As usual, register UD (13) must contain the DCB address. 

4.8.2 Queuing Routines 

The acquisition and release of a resource by a device, such as a selector channel, is known as 
connection and disconnection. If a leaf is already connected, another connection cannot be made. 
The task is put in a wait state and the request is queued. The queue will be handled in priority order 
of the tasks in the queue. This assures a priority execution, and still maintains the chain order of 
first in, first out. As soon as a leaf is disconnected, the next IOB (on the top of the chain) will be 
connected and its wait state will be terminated. 

Three different queueing strategies are available for disk I/O: 

• A FIFO routine, in which the order is defined by the order entry into the queue (COMFIFO). 

• A routine that orders the queue according to task priority (COMQ). 

• A routine that sorts I/O requests is such a way that requires the shortest seek times (DISKQ). 

Effectively, each DCB can specify its own queueing routine. The choice for standard devices is as 
follows: 

The priority-ordered queue routine is selected for non-direct access devices and the seek schedule 
queue routine for direct access devices. Users can supply their own queueing routines by placing the 
routine address in DCB. The queue routine must follow the convention that the request at the top of 
the queue is the next one to be serviced. If no queueing routine is specified (a zero is found) in the 
DCB, the priority -ordered queue routine is the default. There may be a restriction on the registers 
available for use inside the queueing routine. 
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CHAPTER 5 
STRUCTURE OF A DRIVER 



5.1 INTRODUCTION 

OS/32 device drivers are, in general, re-entrant. They are written such that only one copy of the 
actual code can be shared by multiple instances of the supported device. The only exceptions to this 
are quick and dirty prototype drivers or drivers for one-of-a-kind devices. Chapter 6 discusses how 
to generate these data areas. Chapter 7 describes how a separate copy of the device control block 
(DCB) and channel control block (CCB) is generated for each device of this particular type at 
system generation (sysgen) time. 

The code section of a device driver consists of several different types of routines. They are: 

• Input/Output Handlers (IOHs) are routines that run in as nonreentrant system state extensions 
of the SVC1, in registers E8-E15 only. (See Appendix B for a description of operation states). 
These routines are optional as the system will provide a default IOH list (COMIOH). 

• Event Service Routines (ESRs) are subroutines of the system queue service (SQS). A driver may 
have two or three special ESRs and possibly additional intermediate ESRs. These special ESRs 
are: 

— The driver initialization routine (DCB.INIT) entered from SQS when SVC1 schedules a data 
transfer. 

— The driver termination routine (DCB.TERM) selected, by default, when the driver 
initialization routine exits via DIRDONE. The DCB.TERM is entered when an interrupt 
service routine (ISR) adds the device leaf to the system queue to schedule the next ESR. 

— Optionally, the command initialization routine (DCB.FUNC) entered from SQS when SVC1 
schedules a command function. 

• Interrupt Service Routines (ISRs) run as subroutines of the processor microcode in interrupt 
service state, registers EO through E7 only. (See Appendix B for a description of operation 
states.) In effect, they run outside of the operating system as software extensions to the 
processor's interrupt service. To signal events to the operating system, ISRs add device leafs to 
the system queue. 

• I/O Done Executor (DCB.DONE) is an optional routine that is seldom used except by the 
Perkin-Elmer Disk Driver and Contiguous File Manager. If supplied, it runs as a subroutine of, 
or in place of, the standard IODONE routine. In addition to special processing, a device-specific 
IODONE routine would normally perform many of the same functions as the standard 
IODONE (see Chapter 4). 

• Queueing Strategy Routines (DCB.Q) several alternate queuing strategies (priority, first- 
in/first-out (FIFO), seek-scheduling for disks) are supplied by the operating system and are 
sufficient for standard requirements. (See Appendix D for detailed descriptions of queueing 
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routines.) If there are special requirements, these routines must by supplied as part of the driver. 

• Translation Table is supplied if the driver uses the translation option of the auto driver channel 
(or the TRANSLATE command). 

• Special Character Handlers are supplied if the translation table includes special character traps. 
The special character Handlers are routines to handle these traps or interrupts. 

The following sections describe IOHs, ESRs, and ISRs. Standard IODONE and Q strategy are 
discussed in Chapter 4. 

5.2 THE INPUT/OUTPUT HANDLERS (IOH) 

The I/O Supervisor is often called the SVC1 skeleton because it performs only standard request 
validation and input/output block (IOB) allocation/initialization. It then invokes an IOH to execute 
the request. Each device driver has an IOH list, located by a pointer in the device's DCB. An IOH 
list contains an entry for each possible I/O request. The entry will contain the address of the IOH 
for the requested function, if the driver supports that function. Otherwise, the entry will contain the 
address of the SVC1 illegal function exit. 

The IOH list also has entries for special event processing: system initialization, power restore, and 
end-of-task. These special entries are discussed in Chapter 5. 

The system supplies several standard IOH lists and the associated I/O Handlers. These are: 

• the NULL device, 

• the bare disks, 

• and the common IOH list. 

In fact, the contiguous file manager is essentially a sophisticated set of IOH routines that front-end 
the disk driver. The dummy console is also a set of IOH routines that pass console I/O requests to 
the console monitor task for processing. 

IOHs run as extensions of SVC1. Thus, they run in nonreentrant service state and are restricted to 
using registers 8 through IS. There are two basic types of IOH routines - those for requests that 
invoke the device driver and those that handle the requests directly without invoking the driver. 

The IOH routines that invoke the device driver are those for data transfer functions (READ, 
WRITE, TEST and SET) and command functions (REWIND, WRITE FILEMARK, etc.). These 
IOH routines require an IOB and are entered with these register contents: 

R9 = address of task control block (TCB) 
RA = address of IOB 
RB = address of DCB 
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The IOH routines attempt to connect the request to the device (leaf) so that the driver may be 
scheduled. Connection is performed by by copying the IOB into the DCB's embedded IOB and 
placing the DCB address in the leaf. The IOB can then be released, and the driver may be 
scheduled by adding the leaf address to the system queue. See Section 2.S.2.2 for information on 
SQS. 

If the device is busy (i.e, leaf is already connected), the IOB is queued to the leaf unless the SVC1 
function code specified Unconditional Proceed. If the task's IOB free pool is exhausted, the task is 
left in IOB wait. IOH routines exit to label SVC1EXIT. 

The IOH routines for functions that do not invoke the driver do not require IOBs. These functions 
include HALT I/O, TEST I/O COMPLETE, and WAIT ONLY. The entire request is performed 
within the IOH. The following registers are initialized on entry: 

R9 = address of TCB 
RB = address of DCB 



TABLE 1. INPUT/OUTPUT HANDLER (IOH) FORMAT 



IOH .READ 


DS4 


SVC1 read executor 


IOH.WRIT 


DS4 


SVC1 write executor 


IOH.WAIT 


DS4 


SVC1 wait-only executor 


IOH .HALT 


DS4 


SVC1 halt I/O executor 


IOH. TEST 


DS4 


SVC1 test I/O complete executor 


IOH. RE W 


DS4 


SVC1 rewind executor 


IOH.BSR 


DS4 


SVC1 backspace record executor 


IOH.FSR 


DS4 


SVC1 forward space record executor 


IOH.WFM 


DS4 


SVC1 write filemark executor 


IOH.FFM 


DS4 


SVC1 forward filemark executor 


IOH.BFM 


DS4 


SVC1 backward filemark executor 


IOH. EOT 


DS4 


SVC3 task termination execution 


IOH.INIT 


DS4 


Device initialization 


IOH. DDF 


DS4 


Device-dependent function executor 


IOH.CON 


DS4 


Special handler for system console 


IOH.PWR 


DS4 


Special handler for power restore. 



48-190 F00 R00 



5-3 



The IOH is set up via the IOH macro call. 

Some are the concern of SVC1. Others allow for device-specific processing of events like task 
termination, system initialization and power restore. 

The IOH List allows a driver to have custom SVC1 processing and special event processing (such as 
system initialization, power restore, and end-of-task). For most drivers, the SVC1 processing 
provided in the system default IOH List (COMIOH), is sufficient. Many drivers have special 
system initialization and/or power restore processing requirements. These drivers must include their 
own IOH list. 

Custom IOH lists can be included in the driver itself. This is the usual case. If a single custom IOH 
list will serve several drivers, it may be implemented as a separate source module. In either case, 
the label of the IOH list must be an entry point in the source module. 

IOH lists are coded using the IOH macro. Table 5-2 lists the parameters to the IOH macro. The 
NAME parameter provides the label for the IOH list. This is the only required parameter. 

NOTE 

The IOH macro automatically generates a weak entry 
(WNTRY) for the NAME. 

All of the SVC1 function parameters (READ, WRITE, etc.) will default to illegal functions if the 
parameter is omitted. To use the default IOHs (i.e., same as those used by COMIOH), use the 
label given in the last column of Table 5-2. 

NOTE 

These labels must be declared as externals (EXTRN) to the 
driver/IOH module. 



The special IOH entries all default to zero, indicating no special handling. If a driver needs special 
IOH processing (e.g., system initialization), the appropriate parameter is supplied, giving the name 
(label) of the IOH routine. For example, if a driver has a system initialization IOH with label 
DVR.SYSI, the parameter would be supplied as INIT=DVR.SYSI. Other special handlers are 
specified in the same manner. 

All IOHs are entered via a BRANCH and LINK (BAL) instruction on register 8, with the DCB 
address in register 11 (B). Only registers 8 through IS (F) are available. 
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TABLE 2. IOH MACRO PARAMETERS 





SVC 1 




FOR DEFAULT 


PARAMETER 


FUNCTION 


IF OMITTED 


USE 


NAME 




REQUIRED 




READ 


Read 


SV1FCER 


SVC1READ 


WRITE 


Write 




SVC1WRIT 


WAIT 


Wait Only 




SVC1WAIT 


HALT 


Halt I/O 




SVC1HALT 


TEST 


Test I/O 




SVC1TEST 


SET 


Test & Set 




SVC1NOOP 


REW 


Rewind 




SVC1REW 


BSR 


Backspace Record 




SVC1BSR 


FSR 


Forward Record 




SVC1FSR 


WFM 


Write File Mark 




SVC1WFM 


FFM 


Forward File Mark 




SVC1FFM 


BFM 


Backspace File Mark 




SVC1BFM 


DDF 


Device-dependent function 






EOT 


End-of-task 





N/A 


INIT 


System Initialization 







CON 


Console 







PWR 










5.3 DRIVER INITIALIZATION ROUTINE 

The driver initialization routine contains preparation for the I/O transfer. The device is connected to 
the event tree and the physical I/O is started. This phase would, for example, start a seek operation 
for a disk I/O transfer. 

The driver initialization routine is used to establish those aspects of the operation that are not 
themselves time critical but are necessary for the next phase which is the processing of interrupts. A 
typical sequence of events in the driver initialization routine might be: 

• Check that the device is available, i.e., does not give either FALSE SYNC or DEVICE 
UNAVAILABLE status when addressed. 

• Set up the CCB for an auto driver channel operation but without actually starting it. Use these 
guidelines: 

— Place the buffer address and length into CCB.EBO and CCB.LBO. 

— Place A(ISR) into CCB.SUBA. 
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— Initialize the channel command word (CCB.CCW). 

• Set up the interrupt service pointer table (ISPT) entry for the first interrupt service routine 
(ISR). 

• Connect the DCB to the time-out chain, but do not initiate the time-out countdown. 

• Execute the first ISR via a simulate interrupt (SINT) instruction. 

• Terminate the routine by branching to DIRDONE. 

The driver initialization phase is entered at the label INITxxxx, where xxxx is the name of the 
device. On entry to this phase from SQS, register 13 contains the DCB address and register IS 
contains the leaf address. The subroutines used in this phase are TOCHON, EVREL, EVMOD, 
and TOCHOFF. The driver may exit from the phase by branching to DIRDONE or IODONE. 

TOCHON is used to put entries onto the time-out chain and is called via: 

BAL U8 , TOCHON 

There is one entry on the chain per DCB. On entry to the subroutine, register 13 contains the DCB 
address. The subroutine sets the time-out value to X'7FFF' and puts the entry onto the time-out 
chain. 

DIRDONE is used for a successful exit from the initialization phase. No registers need to be 
established before entry. The exit will establish the label TERMxxxx as the current ESR of the 
driver termination phase, i.e., the address of the DCB.TERM is put into the field DCB.ESR, unless 
an ESR has already been established in the initialization phase via the routine EVMOD. 

IODONE is used when the initialization encounters a fatal error or normal termination condition. 
For example, the device might be unavailable (not on-line) as determined by the device status. This 
exit can also be used in the termination phase. 

5.4 INTERRUPT SERVICE ROUTINE (ISR) 

One or more ISRs are responsible for responding to interrupts and for starting any subsequent 
physical I/O operations or event service routines (ESR). For example, if the disk seek has been 
completed, an ISR will be activated, in order to output the data transfer commands to the device. 

ISRs are entered with a program status word (PSW) state of X'28xx'. Only registers through 7 
can be used in an ISR, unless one can guarantee absolutely that all devices the driver will control 
will always be strapped to interrupt at a level lower than 0, at which point registers through 15 
may be used. If registers 8 through 15 of register set are used by an ISR, they are likely to 
destroy any register the operation system is currently using and cause the operating system to crash. 

The ISRs are used for all occasions in which it is undesirable to be interrupted by other operations. 
The first ISR is different from subsequent ISRs because it is entered via SINT instruction. It is 
essentially an uninterruptible subroutine of the driver initialization routine. 
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The ISR are executed in the interrupt state (IS-STATE). Entry into these is made on the basis of a 
resultant hardware interrupt of the device, or by carrying out a SINT command. Normally all I/O 
commands are executed in the ISRs. Another ISR can be run for the next interrupt of this device, 
when the corresponding address in the ISPT or the CCB is being modified. The ISR should be 
written in pure reentrant code. 

A typical sequence of events in the first ISR might be: 

• Check the condition code to determine why you are in the ISR routine. 

• Start the time-out countdown by setting a value in DCB.TOUT. 

• Prepare the device for transfer (OC DEV ADD .COMMAND). 

• Transfer a byte of data. 

• Set up the CCB subroutine address (SUB A) for the next ISR. 

• Start the auto driver channel by modifying the channel command word (CCW), enabling 
interrupts and attempting the first READ or WRITE on the device. Set the execute bit in the 
CCW. 

• Return to the driver initialization routine via the instruction LPSWR EO. 

Because the first ISR returns to the driver initialization routine, it is possible to return state 
information via the PSW condition code in register EO. If, for example, the initial ISR determines 
that the I/O cannot proceed for one reason or another, it is more efficient to abort the I/O in the 
driver initialization routine, rather than schedule an ESR to handle termination. The first ISR can 
accomplish this setting an appropriate error status in the DCB and setting a bit in the condition code 
of the old PSW in EO. When control returns to the driver initialization routine (i.e, when the ISR 
performs LPSWR EO), the driver initialization routine can branch on condition to DIRDONE (no 
error) or IODONE (error). 

Subsequent ISRs deal with the transfer of data, error detection or other special conditions. For 
example, the SUBA, which typically would be set up for the next ISR, is given control when the 
buffer is empty. This ISR will also be involved when the device gives a bad status. The ISR might 
perform the following operation: 

• Check the condition code for X'01' (bad status) - in which case the status should be returned to 
the calling program and the operation terminated. 

• Check the condition code for X'02' - schedule termination ESR to return status to the caller and 
terminate I/O operations. 

• Check to determine whether the device timed out with the following: 
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L E5,CCB.DCB(E4) Fetch DCB address 
LH E6, DCB. TOUT (E5) Fetch timer value 
BZ TIMEOUT If zero, branch to set time-out status 



ISRs should be kept as short as possible (15 to 25 instructions). 

During their execution, only higher level I/O interrupts can be serviced. If the ISR disables all 
interrupts, then no interrupts can occur. 

ISRs are entered with a PSW state of X'28xx'. Only registers through 7 can be used in an ISR, 
unless one can guarantee absolutely that all devices the driver will control will always be 
strapped to interrupt at a level lower than 0, at which point registers through IS may be used. 
If registers 8 through IS of register set are used by an ISR, they are likely to destroy any 
register the operating system is currently using and cause the operating system to crash. 

5.5 FINAL INTERRUPT SERVICE ROUTINE (ISR) 

The final ISR disarms the device interrupts and places the leaf address on top of the system queue 
with an ATL instruction. A typical sequence of events in the final ISR might be: 

• Check the condition code to determine why you are in the final ISR routine. 

• Place the status code in DCB.STAT and DCB.DDPS 

• If DCB.TOUT=0 then a time-out has occurred. If a time-out has not occurred, place -1 into 
DCB.TOUT. 

. Schedule TERMxxxx by ATL A(LEAF),SQ. 

• Disarm the device. 

• Return to operating system. 

5.6 EVENT SERVICE ROUTINE (ESR) (INTERMEDIATE AND TERMINATION) 

The driver ESRs are a collection of routines for intermediate operations and for terminating the I/O 
operation. In driver termination, the status of the operation is put into the DCB.STAT so that it 
may be sent back to the calling program's parameter block status halfword. 

Driver termination is entered when an ESR has been scheduled from the system queue. An ESR 
may also be entered because of a time-out. 

An entry put on the time-out chain in the initialization phase has to be removed in driver 
termination. 

Failure to do this can result in a error condition that can cause a system crash. 
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A typical sequence of events in an ESR would be: 

• Check for time-out. Is the countdown value 0? (DCB.TOUT) 

• Check for a HALT I/O operation from the calling program. (DCB.TOUT = zero and 
DFLG.HIB set in DCB.FLGS) 

• Return the I/O operation status and length of transfer to the DCB. 

• Exit via branching to routine IODONE or EVRTE if I/O is to continue. 

When ESRs are executed in the termination phase of the driver, the only subroutine called is 
TOCHOFF. Termination ESRs always end by branching to IODONE, or EVRTE if I/O is to 
continue. 

TOCHOFF is called to remove an entry from the time-out chain via: 

BAL U8, TOCHOFF 

On entry, register 13 or UD contains the DCB address. Registers 10 and 11 are destroyed. 
Intermediate ESRs are used to: 

• modify CCB.SUBA for the next ISR. A SINT can be used to get it started. 

• disconnect the DCB from upper level nodes in the event coordination table. 

• modify DCB.ESR. (SQS uses the address in DCB.ESR as the entry point into the driver when 
the A(LEAF) is removend from system queue.) 
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CHAPTER 6 

COMPONENTS OF THE DEVICE CONTROL BLOCK (DCB) 
AND CHANNEL CONTROL BLOCK (CCB) 

8.1 INTRODUCTION 

The DCB and associated CCBs are the device driver data and control areas. There is usually one 
DCB definition for each type of device. Each type of DCB is assigned a device code or DCOD. The 
DCOD is used to select DCBs (and drivers) when configuring the system, as described in Chapter 
7. 

DCODs zero through 239 and 255 are either already assigned or reserved for use by Perkin-Elmer. 
DCODs 240 through 254 are available for user -written drivers. As mentioned above, it is by DCOD 
that devices are configured into the system. The DCOD selects a DCB type corresponding to the 
device. The DCB, in turn, selects which driver will be included to handle the device. 

When more than one device of the same type are configured, multiple DCBs (and CCBs) of the 
same type are generated. DCBs are generated by assembling DCB macro calls that are produced by 
the system generation utility (SYSGEN/32) with parameters supplied in the configuration 
statements. The remainder of this chapter describes the components of these DCB and CCB macros. 

A DCB macro has a name of DCBnnn where n is a 3-digit device code (from 240 to 254). The 
macro must be written to generate a customized DCB each time it is called, based on the 
parameters supplied. The macro must reserve storage for and initialize fields in the device- 
independent and device-dependent portions of the DCB. It must also reserve storage for and 
initialize any CCB used by the driver. The DCB macro is made up of the following sections: 

• The macro prototype statement - giving the macro name (DCBnnn) and the list of valid keyword 
parameters. 

• The macro variable declarations and initializations. 

• Environment initialization (USERINIT). 

• Unique DCB ID generation (%IDVAL). 

• Object module label generation (PROG). 

• Storage allocation and initialization for the DCB (DCBI) and CCB(s) (CCBI). 

• Device Mnemonic Table and Device Leaf Linkage. 

• Miscellaneous (optional) storage allocation and storage initialization. 

. Macro termination (USEREND/MEND). 

Each of these items is covered in the following subsections. Additional information and examples 
are given in the DCBFORM sample macro included with the OS/32 software package in the 
SYSGEN32.MLB macro library. A listing of DCBFORM is included in Appendix C. 
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ft.2 THE MACRO PROTOTYPE STATEMENT 

The macro prototype follows the macro statement and gives the macro name (DCBnnn) and the list 
of valid parameters. The following parameters are required and will always be supplied by 
SYSGEN/32. 

%DCOD is the device code. The device code is used as an ASCII string to form the DCB name. 
The device code also is placed in the DCB structure as a half word value, where it can 
be accessed by the driver to control the execution sequence of the driver. 

%DN is the device address (i.e., the physical device address on the multiplexor (MUX) bus 

to which the device controller responds). It initializes the DCB.DN field. 

%ILVL is the device's interrupt priority level. 

%NAME is the device mnemonic, a 1-4 character device name. 

%IOP is the input/output processor (IOP) number and is provided only if the device is under 

an IOP in a 3260 System. 

A complete list of parameters and their meaning is given in Table 6-1. A more complete description 
is given in the SYSGEN/32 manual in the discussion of the devices statement. 

TABLE 6-1. MACRO PROTOTYPE STATEMENT PARAMETERS 



PARAMETER 



%DCOD 

%DN 

%CLAS 
%ILVL 

%NAME 



SYSGEN/32 
OPTION 



DCOD 

ADDR 

IOCLASS 

ILEVEL 

NAME 



%QU 


QUEUE 


%CONS 


CONSOLE 


%SLCH 


SELCH 


%CNTR 


CONTROLLER 


%IOP 


IOP 


%XDCD 


XDCOD 


%SPND 


SPINDLE 


%RECLN 


RECLEN 


%SPCR 


READCONTROL 



DESCRIPTION 



Device code; also used to create 

unique DCB & CCB names. 

Device address 

I/O class level 

Interrupt level 

Device mnemonic used in naming 

device DCB & CCB in Device Mnemonic Table (DMT). 

Queue scheduling routine for disks 

Flags console device 

Selector channel address 

Device controller address 

Processor number where device resides 

Extended device code. 

Specifies spindle for floppy disks 

Record length 

Read control character sequence 



6-2 
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SYSGEN/32 






PARAMETER 


OPTION 


DESCRIPTION 




%SPCW 


WRITECONTROL 


Write control character sequence 




%TV1 


SCREEN -TIME 


Time for entire screen 




%TV2 


RESPONSE-TIME 


Time for term response 




%XLT 


TRANSLATE 


Name of translation table 




%PDCT 


PADCOUNT 


Padcount value 




%LDCT 


LEADSYNC 


Leading sync, count 




%SHCCB 




Flag for shared CCB 




%POLMT 


POLLIMIT 


Poll limit value 




%EOV 


EOV 


End-of -volume flag 




%CLOCK 


CLOCK 


Clock value 




%SIZE 


SIZE 


Page size for pseudo-devices 




%DUAL 


DUAL 


Dual port option 




%CM 


CM 


Channel manager address 




%ITV 


INTIMER 


Input device timer 




%IOLM 


IOLIMIT 


Error retry for I/O 




%SLS 


LINESTATUS 


Static line status 




%MNOF 


MAXFRAMES 


Max frames outstanding 




%MBFS 


MAXWRITEBUF 


Maximum buffer size 




%MRBS 


MINREADBUF 


Minimum record buffer size 




%MTO 


MTO 


Master time-out 




%N2 


N2 


No response 




%NC 


NCS 


Numbered commands 




%OTV 


OUTTIMER 


Output device timer 




%PLDT 


POLLDELAY 


Poll delay timer 




%PLTC 


POLLTIME 


Poll time out 




%SSA 


SSA 


Sec station address 




%T1 


T02 


Tl timer for X.25 




%UCSI 


UCSI 


UNNUM cmds input 




%UCSO 


UCSO 


UNNUM cmds output 




%WKTC 


WAKEUP 


Wakeup time-out 






NODISK 


Suppresses DA parameter in EVNGEN macro call. 






DISK 


Causes DA parameter in EVNGEN macro call. 






NONSHARED 


Suppresses %SHCCB parameter in 
DCB macro call 






USER 


User-defined parameters 
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In addition to these parameters which are known to SYSGEN/32, additional device-dependent 
parameters may be specified. These "USER" parameters may be supplied at sysgen time via the 
"USER=" parameters on the device specification statement. The following is an example of the 
DCB macro prototype statement. 

NOTE 

Macro continuation lines are indicated by a non-blank 
character in column 72. This character will not appear on 
Common Assembly Language (CAL) listings. 

MACRO 

DCB241 %DCOD=,%DN=,%NAME=,%CLAS=, x 

%ILVL=, %RECLN=, %XDCD=, %PEN= 

Two optional parameters (%RECLN and %XDCD) and one USER parameter (%PEN) can be 
specified. It is possible to supply default values for any of the optional parameters. For example, 
%RECLN=256. 

The %XDCOD field may assume whatever significance a particular device driver wishes to assign 
to it. For example, in some Perkin-Elmer supplied drivers, the %XDCD field is used to specify the 
baud rate and parity of a communications line. 

After the DCB macro prototype statement, all local and global macro variables must be declared. 
Two are required: 

BGBLA %IDnnn is a batch global arithmetic variable that counts DCBs of type nnn (=device 
code) - starting at zero. 

GBLC %IDVAL is a global character variable that contains the ASCII representation of the 
current value of %IDnnn. It is used to generate unique DCB labels of the term 
DCBnnnid. 

Other local and global macro variables may be declared and initialized as required by the 
structure/logic of the particular DCB macro. See the examples in DCBFORM in Appendix C. 

6.3 ENVIRONMENT INITIALIZATION 

After the macro variable declarations and initializations, the DCB macro for custom drivers must 
call the USERINIT macro. This macro resets various macro flags to initialize the macro 
environment. In particular, it resets flags that indicate that the structure definition macros have 
already been included. If DCB or CCB field names are undefined in a user-written DCB macro 
(during the macro/assembly phase of system generation), check the macro definition to ensure that 
USERINIT is invoked at the appropriate place in the macro. See Appendix C for the DCB macro 
definition. 
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At this point it is also a good idea to pull in the structure of the device-dependent part of the DCB. 
Presumably such a structure is defined when writing the driver code. This provides the symbolic 
field definitions for the miscellaneous field initialization section of the macro. It also provides the 
total size of the DCB for the DCBI macro. For example, if the device is a plotter with a device- 
dependent DCB defined in $PLTRDCB: 

USERINIT initialize macro variables 

$PLTRDCB include device-dependent DCB definition 

$PLTRDCB must reside in the USERDLIB.MLB macro library along with the DCB macro itself. 

6.4 UNIQUE DCB ID GENERATION 

This section of the DCB macro generates the unique ASCII ID value (%IDVAL) and increments 
the counter %IDnnn. This is accomplished as follows. First, the current value of %IDnnn is 
converted to ASCII in %IDVAL using the macro CONVNUM: 

CONVNUM VAL=%IDnnn 

Then, the value of %IDnnn is incremented by one for the next device of this type (if any): 

%IDnnn SETA %IDnnn+l 

%IDVAL can now be used to generate unique DCB/CCB labels. For. example: 

DCB%DCOD%IDVAL EQU * 

or 

CCB%DCOD%IDVAL EQU * 

Because the sequence %DCOD%IDVAL appears frequently within the macro, it is often 
advantageous to define a local character macro variable and initialize to the value 
%DCOD%IDVAL. For example, 
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LCLC %OFFS 



%OFFS SETC '%DCOD' : '%IDVAL' 

The variable %OFFS can then be used in place of %DCOD%IDVAL. 

6.5 OBJECT MODULE LABEL GENERATION 

Each user-written DCB is assembled as a separate unit, producing a labeled object module for each 
device. The object module is given a name via the "PROG" statement, as follows: 

DCB%NAME PROG DCB program label for link map. 

%NAME is the device mnemonic passed by SYSGEN/32. 

8.6 DEVICE CONTROL BLOCK (DCB) STORAGE ALLOCATION/INITIALIZATION 

This section is the heart of the DCB macro. A utility macro, DCBI, is used to reserve the storage 
and perform specified initialization. The parameters to DCBI and the DCB fields that they initialize 
are listed in Table 6-2. A listing of the DCBI macro is included in Appendix C. 
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TABLE 6-2. DCBI PARAMETERS AND INITIALIZED FIELDS 



DCBI 


DEFAULT 


" DCB 




PARAMETER 


VALUE 


FIELD 


COMMENTS 


%FUNC 





DCB.FUNC 


Command driver entry 


%INIT 




DCB.INrr 


Data transfer driver entry 


%TERM 




DCB.TERM 


Termination ESR entry 


%ATRB 





DCB.ATRB 


Supported attributes 


%IOC 





DCB.CLAS 


Accounting class 


%RECL 





DCB.RECL 


Record length 


%TOUT 


X'7FFF' 


DCB.TOUT 


Initial time-out constant 


%FLGS 


DFLG.LNM 


DCB.FLGS 


Device flags 


%DCOD 




DCB.DCOD 


Device code 


%IOH 


COMIOH 


DCB.IOH 


Address of IOH list 


%DA 




DCB.DIRL 


Points to DIR%DCOD%ID 






DCB.BETL 


Points to BIT%DCOD%ro 


%CLOC 




DCB.CCB+6 




%CC4 




DCB.CCB+4 




%DSIZE 




DCB.SIZE 


Disk size in sectors 


%STRK 




DCB.STRK 


Sectors per track 


%TCYL 




DCB.TCYL 


Tracks per cylinder 


%BMSA 




DCB.BMSA 


Bitmap buffer required 


%DRSA 




DCB.DRSA 


Directory buffer required 


%DSC 




DCB.DSC 




%NUM 




DCB.NUM 




%PFUN 




DCB.PFUN 




%PXLT 




DCB.PXLT 


Card reader/punch punch 
translation table 


%RXLT 




DCB.RXLT 


Card reader/punch read 
translation table 


%PSEP 




DCB.PSEP 


Card reader/punch punch 
separate 


%EOLC 




DCB.EOLC 


End of line characters for 
line printer 


%RTRY 




DCB.RTRY 


Operation retry counter 


%SHCC 





DCB.CCB 


If not 0, define first CCB 
pointer 


%CCB 




DCB.CCB+4 


If not and %SHCC not 0, 
then define second CCB pointer 


%EDMA 





DCB.EDMA 




%COPY 


$DCB$ 




Used to copy structure 


%SIZE 


DCB.DVDP+4 




Size in bytes of DCB 


%IOP 





DCB.IOP, DCB.ISP 


Sets up parameter dependent 






DCB.SQ 


fields in the DCB. | 
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The following DCBI macros are of particular importance: 

DCOD* is the device code for this DCB. 

SIZE is the amount of storage to be reserved for the DCB. This parameter defaults to the size 

of the device-independent DCB plus 4 bytes. 

EMIT* is the name of the device driver data transfer initialization entry point (e.g., INITxxxx). 

TERM* is the name of the device driver termination event service routine (ESR) entry point 
(e.g., TERM=TERMxxxx). 

FUNC is the name of the device driver command initialization entry point (e.g., 
FUNC=CMDxxxx). 

IOH is the name of the device driver input/output handler (IOH) list (e.g., IOH=IOHxxxx). 

ATRB* supported SVC1 function codes for DCB.ATRB (e.g., ATRB=7B80). 

ID* is used to pass IDVAL for unique label generation (e.g., ID=%IDVAL). 

IOP is the processor number where the device resides. 

The parameters marked with an asterisk are required parameters to DCBI. The INIT/TERM 
parameters are important because reference to the driver entry points by the DCB is the mechanism 
for including the appropriate driver to handle the device. 

Other parameters to DCBI may be derived from parameters to the DCBnnn macro (e.g., 
RECL=%RECLN) or set as constants within the DCDnnn macro (e.g., RECL=80). Table 6-2 lists 
the defaults for other parameters. Any parameter (or DCB field) that is not specified and that does 
not have a default will be initialized to zero. 

Example: 

DCBI DC0D=241,SIZE=PLTRDCB,INIT=INITPLTR, x 

TERM=TERMPLTR,FUNC=CMDPLTR / ATRB=7BC0, x 

IOH=IOHPLTR, ID=%IDVAL 

Additional device-dependent DCB initialization and optional storage allocation/initialization is 
discussed later in this chapter. 

8.7 CHANNEL CONTROL BLOCK (CCB) STORAGE ALLOCATION/INITIALIZATION 

All OS/32 device drivers that handle interrupts require at least one CCB. Some devices such as full- 
duplex communication controllers require two CCBs (one for transmit and one for receive). The 
CCBI macro will allocate or initialize one CCB on each call. A second call to CCBI is allowed to 
generate the second CCB, where required. 

There are two required parameters to CCBI: 
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• DCOD - the device code 

. ID - the current IDVAL (e.g., ID=%IDVAL) 

These parameters are used for generating a unique CCB label (CCBnnnid), and for referencing the 
DCB (as DCBnnnid). Optional parameters are listed in Table 6-3. These parameters initialize 
fields in the CCB. Normally, CCB fields are set up dynamically by the device driver. 

TABLE 6-3. OPTIONAL PARAMETERS FOR CCBI MACRO DEFINITION 



CCBI 


CCB 




PARAMETER 


FIELD 


COMMENTS 


%XLTAB 


CCB.XLT 


Translation table 


%SUBA 


CCB.SUBA 


ISR Address 


%EBO 


CCB.EBO 


Buffer End Address 


%CCW 


CCB.CCW 


Channel Control Word 


%CFLGS 


CCB.FLGS 


Driver-dependent flags 


%CCBN 


N/A 


Must be undefined for first CCB 



When calling CCBI to generate a second CCB, the parameter %CCBN must be specified - any value 
will do (e.g., CCBN=2). The second CCB will be named "CCXnnnid." Also, when two CCBs are 
generated, the DCBI macro parameter CCB should be specified to cause the second CCB to be 
referenced by the DCB. 

Example of first or only CCB: 



CCBI DC0D=241 , I D= IDVAL, XLTAB=XLTPLTR 



Example of a second CCB, if required: 



CCBI DC0D=241 , ID=IDVAL, CCBN=X 



Note that any value of CCBN is acceptable as long as the parameter is defined. The value itself is 
ignored. 

6.8 DEVICE MNEMONIC TABLE (DMT) AND LEAF LINKAGE 

For the DCB to be located via the DMT, a special label and entry point must be generated as 
follows: 
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DCB_%NAME EQU DCB%DCOD%IDVAL 
ENTRY DCB_%NAME 



This generates an alternate name for the DCB that can be referenced by the DMT macro generated 
by SYSGEN/32. For example, if a device is named "PLTR" for a plotter, the alternate DCB name 
would be DCB_PLTR. 

After generating the label for the DMT, it is also necessary to initialize the DCB.DMT field to 
reference the DMT entry for this device: 

ORG DCB%DCOD%IDVAL+DCB.DMT 
EXTRN DMT_%NAME 
DAC DMT_%NAME 

The label DMT_%NAME is generated by the DMT macro as an entry point. 

The DCB.LEAF field must be initialized to point to the correct device leaf. If the device shares a 
leaf with other devices, the parameter %SHCCB will be nonnull. In this case the name of the leaf is 
LF%SHCCB. Otherwise, the leaf name is LF%DCOD%IDVAL. The leaves and their labels are 
generated by the EVNGEN macro emitted by SYSGEN/32. 

The following code sequence initializes the DCB.LEAF field: 

ORG DCB%DCOD%IDVAL 

AIF (T'%SHCCB' EQ 'U'J&NSLEAF 

EXTRN LF%SHCCB 

DAC LF%SHCCB 

AGO &NRMLFX 
&NSLEAF ANOP 

EXTRN LF%DCOD%IDVAL 

DAC LF%DCOD%IDVAL 
&NRMLFX ANOP 

Note that if this will never be used with shared leaves, the conditional (AIF), the references to 
LF%SHCCB and AGO%NRMLFX can be omitted. 

6.9 MISCELLANEOUS (OPTIONAL) STORAGE ALLOCATION/INITIALIZATION 

This section of the DCB macro generates any optional storage outside of the DCB itself. For 
example, the driver might require a work buffer whose size is specified as a sysgen parameter and 
therefore cannot be part of the fixed length device-independent DCB structure. 
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This section also performs optional initialization of fields in the DCB (usually the device-dependent 
part), such as Extended Device Code (XDCD) or pointers to optional storage discussed above. 
Some of the initialization may be driven by parameters supplied at sysgen time. For example: 

AIF(T"XDCD EQ 'U'J&NOXDCD 
ORG DCB%DCOD%IDVAL+DCB.XDCD 
DC %XDCD 
&NOXDCD ANOP 

This code initializes DCB. XDCD if a value was specified. Otherwise, the field is left at zero. 

Other initializations may be required. For example, suppose the driver requires a variable length 
buffer, specified by USER parameter %BUFL (default 256). The following code might be used: 

ORG DCB%DCOD% I DVAL + DCB . BUF S 

DAC BF%DCOD%IDVAL start of buffer 

DAC BFE%DCOD%IDVAL end of buffer 

This will set up the buffer start and end addresses in the device-dependent DCB. The buffer would 
be allocated as follows: 

ORG $ST%DCOD%IDVAL end of DCB 
ALIGN 4 (if required) 

BF%DCOD%IDVAL EQU * 

AIF(T'%BUFL EQ 'U')&BUFDFL use default 
DS %BUFL specified size 

AGO &BUFF 

&BUFDFL ANOP 

DS 256 default size 

&BUFF ANOP 

BFE%DCOD%IDVAL EQU *-l 

$ST%DCOD%IDVAL EQU * redefine end address 



48-190 F00 R00 6-11 



Note that label $ST%DCOD%D>VAL is defined by the DCBI macro as the first location after the 
end of the device-dependent DCB. When allocating additional storage, this label should be 
redefined as shown. 

6.10 MACRO TERMINATION 

After all miscellaneous initializations have been completed, all that remains is to properly terminate 
the DCB. This requires three steps. 

1. "ORG" to the end of the DCB or any allocated storage (label $ST%DCOD%IDVAL). 

2. Invoke the USEREND macro. 

3. Code the MEND (Macro End) statement. 
The following is the required code: 

ORG $ST%DCOD%IDVAL 

USEREND 

MEND 
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CHAPTER 7 
DIFFERENCES FOR DRIVERS WRITTEN UNDER INPUT/OUTPUT PROCESSORS (IOP) 

7.1 INTRODUCTION 

Users of the 3260 System have available to them the 3200 IOP which performs physical input/output 
(I/O) to the devices configured under it. The purpose of the IOP is to minimize the amount of time 
the central processing unit (CPU) has to spend performing I/O functions, thereby enabling the CPU 
to perform other operating system services or execute user tasks in a more efficient manner. 

A 3260 System can have up to nine satellite processors which can be a mixture of auxiliary 
processing units (APU) and IOPs. The devices in a 3260 System can reside either under an IOP (or 
multiple IOPs), the CPU or both. Note that the system console and all Integrated 
Telecommunication Access Method (ITAM) devices (including the direct memory access 
input/output subsystem (DIOS)) must reside on the CPU. It is possible for a single copy of a device 
driver in memory to support devices that reside under multiple processors. In fact, Perkin-Elmer's 
standard device drivers have this capability. 

This chapter will discuss the techniques a driver writer should use so that the driver can execute 
under both the CPU and IOPs. 

7.2 CENTRAL PROCESSING UNIT (CPU) INPUT/OUTPUT PROCESSOR (IOP) 
DIFFERENCES 

There are several ways in which the IOP differs from the CPU in a 3260 System. The first 
difference is that the IOP has an interrupt service pointer table (ISPT) that has fullword entries and 
can be located anywhere in memory. The CPU's ISPT has halfword entries and is always located at 
memory address X'DO'. Therefore channel control blocks (CCBs) and interrupt service routines 
(ISRs) are not restricted to the first 64KB of memory. A pointer to the ISPT for each IOP is 
located in its input/output parameter block (IPB). 

The second difference is an optional fullword CCB.SUBA field as specified by bit 9 in the channel 
command word (CCW). (See Fig 2-6 and accompanying description of CCB.) Therefore, the ISR 
address specified by the CCB.SUBA field is not restricted to the first 64KB of memory. Currently, 
this 64KB limit still exists for standard Perkin-Elmer device drivers, as they have not been 
modified to use this particular feature of the IOP. 

The third difference is the use of a multiple level type of system queue service (SQS) called 
synchronous interrupt service (SIS). Drivers configured under the IOP should not attempt to access 
the standard system queue of the CPU. On the CPU, leaf structures are added to the system queue 
to be serviced. On the IOP, the leaf structure must be added to the level 4 synchronous interrupt 
queue. 

Mechanisms are provided to handle the differences between the CPU and the IOP, as described 
below. 
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7.3 BUILDING THE DEVICE CONTROL BLOCK (DCB) 

There are a number of new fields in the DCB that play a significant role in the proper operation of 
a driver due to the addition of the IOP. These fields are: 

DCB.IOP is the id number of the processor where the device resides; RTSM id for IOP 

devices; zero for CPU devices. 

DCB.ISP is the address of the ISPT for the processor where the device resides. This address is 

variable for IOP devices and X'DO' for CPU devices. 

DCB.SQ is the address of the proper system queue for the processor where the device resides. 

This field is also the address of the synchronous interrupt queue level 4 for IOP 
devices and the address of the standard system queue for CPU devices. 

These fields must be set up at system generation (sysgen) time by the macros that build each DCB. 

The Sysgen/32 task has been modified to recognize devices that are under an IOP and user-written 
drivers are included in the operating system using the standard Sysgen/32 mechanism. See the 
SYSGEN/32 Reference Manual for more details. 

The user-written DCB must set up the new DCB fields described above. The Sysgen/32 task will 
add a new parameter to all device macro calls which is the id number of the processor where the 
device resides if it is under an IOP. Therefore the user should add an "IOP=0" parameter to the 
macro prototype statement of the user DCB macro. The zero is the default value, indicating the 
CPU. If the user DCB macro calls the DCBI macro provided by Perkin-Elmer to set up many 
standard DCB fields, the user only has to add a "IOP=%IOP" parameter to the parameter list in the 
DCBI macro call. If the user DCB macro sets up the DCB fields itself, the following code must be 
added to the macro to set up the new fields. These macro statements will follow the 

ORG $ST%DCOD%ID 

line at the end of the standard DCBI definition as shown in Appendix C. 



7-2 48-190 F00 R00 



AIF 


(*%IOP' EQ 'O'J&NOIOP 


Branch if on CPU 


ORG 


D%SYSINDX+DCB. IPB 




DAC 


A(IPB%IOP) 


IPB address 


EXTRN 


IPB%IOP 




ORG 


D%SYSINDX+DCB.ISP 




DAC 


A(ISPS%IOP) 


ISPT address 


EXTRN 


ISPS%IOP 




ORG 


D%SYSINDX+DCB.SQ 




DAC 


A(SIQ%I0P:4) 


system interrupt 


EXTRN 


SIQ%I0P:4 




ORG 


D%SYSINDX+DCB . IOP 




DCZ 


%IOP 


I OP number 


AGO 


&IOPEXIT 


Done, branch out 


&NOIOP 


ORG D%SYSINDX+DCB.SQ 




DAC 


SQ 


CPU system queue 


EXTRN 


SQ 




ORG 


D%SYSINDX+DCB.ISP 




DAC 


X'DO' 


CPU ISPT address 


ORG 


D%SYSINDX+DCB.IOP 




DCZ 





Not on IOP 


&IOPEXIT 


ANOP 


Finished 



7.4 CODE CHANGES 

In the driver code itself, the only problems the programmer should encounter is when the driver 
must access the system queue (e.g., to schedule the leaf in an ISR) or modify the entry in the ISPT. 
Two macros have been provided that reside in the SYSMACRO.MLB provided by Perkin-Elmer 
that enable a driver to be written in a manner that is transparent to the processor. 

7.4.1 Add to System Queue Macro (ADDSQ) 

For all Series 3200 Processors, except the IOP on the 3260 system, the following instruction is used 
by a device driver to add an item to the system queue: 

ATL Rx,SQ 

On an IOP, this instruction will not produce the desired result, since the IOP Event Service (ES) 
state is not driven by the system queue data structure. In addition, the IOP, like all other 3200 
Series processors, does not generate internal system queue service interrupts. 
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Thus, the ADDSQ macro is provided. This macro will take the item (typically a leaf) and add it to 
the queue pointed to by the field DCB.SQ. 

Calling convention: 



label 



ADDSQ I TEM=Rx , DCB=Ry , WORK=Rz 



Where: 

Rx is a register that contains the address of the item to add to the processor's queue. 

Ry is a register that contains the address of the DCB. 

Rz is a work register. 

This macro will generate the following code, which is compatible with both the IOP and the other 
3200 Series processors: 



Rz,DCB.SQ(Ry) 



BNZ 


LABEL1 


LA 


Rz,SQ 


LABEL1 


EQU * 


ATL 


Rx,0(Rx) 


EPSR 


Rz,Rz 


TI 


Rz,PSW.NTM 


BZ 


LABEL2 


LIS 


Rz,4 


PINT 


Rz 


LABEL 2 


EQU * 



Get queue pointer 

If O, implies standard SQ, 

so get standard SQ address 

Add the item to the queue 
Get current PSW 
If bit 15 on, we are on IOP 
If on CPU, then exit 
If on IOP, then start 
Queue service running 
Done 



7.4.2 Interrupt Service Pointer Modification (ISPMOD) 

For all Series 3200 Processors, except the IOP on the Model 3260 System, the following instruction 
is used by a device driver to modify the ISPT: 

STH Rx,ISPT(Rz,Rz) 

On an IOP, this instruction will not produce the desired result, since the IOP ISPT is not located at 
"ISPT"(X'D0'), and is not half word-indexed. Thus, the ISPMOD macro is provided. 
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The ISPMOD macro takes the value in Rx and places it in the proper entry in the ISPT (based on 
device address). On the CPU, each entry is a halfword. On an IOP, each entry is a fullword. 

Calling convention: 



label 



I SPMOD I TEM=Rx , DCB=Ry , DN=Rz , WORK=Rm 



Where: 

Rx is a register that contains the value that should be placed in the ISPT. 

Ry is a register that contains the address of the DCB. 

Rz is the device address. 

Rm is a work register. 

This macro will generate the following code: 



EPSR 


Rm,Rm 


TI 


Rm,PSW.NTM 


BZ 


LABEL1 


SLLS 


Rz, 2 


L 


Rm,DCB.ISP(Ry) 


ST 


Rx,0(Rm,Rz) 


SRLS 


Rz, 2 


B 


LABEL 2 


L ABE LI 


SLLS Rz , 1 


L 


Rm,DCB.ISP(Ry) 


STH 


Rx,0(Rm,Rz) 


SRLS 


Rz,l 


LABEL 2 


EQU * 



Get current PSW 

Test for being on CPU or IOP 

I f on CPU, go do usual code 

I f on IOP, make up fullword index 

Get address of IOP's ISPT 

Modify the ISPT 

Restore register value 

and exit 

On CPU, make up halfword index 
Get address of CPU's ISPT 
Modify the ISPT 
Restore the register contents 
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APPENDIX A 



DESCRIPTION OF DATA STRUCTURES 



TABLE A-l. DEVICE CONTROL BLOCK (DCB) 



DISPLACE- 
MENT INTO 
STRUCTURE 



0(0) 



4(4) 



8(8) 



LABEL 



DCB.DMT 



DCB.LEAF 



DCB.WCNT 



10(A) 



12(C) 



DCB.RCNT 



DCB.FLGS 



EXPLANATION 



Fullword address of the device 
mnemonic table entry. 

Fullword address of LEAF 



Half word value reflecting the number 
of logical units currently assigned for 
write operation. If this value is -1, a 
logical unit is assigned for exclusive 
write. If this value is 0, no logical units 
are assigned for writes. If this value is 
greater than zero, this number 
represents the number of logical units 
assigned for a write operation. 



Half word value reflecting the number 
of logical units currently assigned for a 
read operation. Reference DCB.WCNT 
for the meaning of the specific values in 
this field. 



Fullword value reflecting the various 
states of the device. Breakdown of this 
fullword value — 



Bit 


1 
2 
3 



Meaning 

bulk device 

on-line device 

system message to console device 

Event service routine (ESR) waiting 

for driver initialization routine to 

complete 

active I/O time-out before driver 

initialization routine done 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 






5 delete pseudo device control block 
(DCB) 

6 console identifier 

7 uncancellable device 

8 SVC6 connection table 

9 write protected device 

10 ITAM supported device 

11 assigned for SVC 15 access 

12 SVCl halt I/O 

13 time-out due to power fail 

14 multiple DCB 

15 pseudo DCB bit 

16 supports vertical forms control (VFC) 

17 power fail, no I/O outstanding 

18 MMD type disk 
19-31 reserved 


16 (10) 


DCB.1INC 


Indicates that this device is being 
intercepted on an SVCl level. 


20 (14) 


DCB.7INC 


Indicates interception on SVC7. 


24 (18) 




Reserved 


25 (19) 


DCB.DCOD 


Byte value reflecting the device code for 
this device. 


26 (1A) 


DCB.DN 


Halfword value reflecting the hardware 
wired address of this device. 


28 (1C) 


DCB.ATRB 


Halfword value reflecting which 
functions this device supports. The 
FMS7 module uses this field at 
ASSIGN time. Breakdown of this 
halfword value — 
Bit Meaning 

interactive 

1 supports read 

2 supports write 

3 supports binary 

4 supports wait I/O 

5 supports random 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 






6 supports unconditional proceed 

7 supports image 

8 supports halt I/O 

9 supports rewind 

10 supports backspace record 

11 supports forward space record 

12 supports write filemark 

13 supports forward space filemark 

14 supports backspace filemark 

15 reserved 


30 (IE) 


DCB.RECL 


Halfword value reflecting the record 
length of this device. 


32 (20) 


DCB.INIT 


Fullword address of driver entry point 
for data transfer request. 


36 (24) 


DCB.FUNC 


Fullword address of driver entry point 
for a device suported command request. 


40 (28) 


DCB.TERM 


Fullword address of driver entry point 
for termination routine. 


44 (2C) 


DCB.TOUT 


Halfword value reflecting the 
maximum amount of time any data 
transfer should take. If this field 
contains X'7FFFF', a time-out condition 
does not start. If this field contains 
X'FFFF' (-1), the transfer completed 
without a time-out condition. If this 
field contains X'0001' and X'7FFE\ the 
system (LFC) clock decrements this 
field by one second until this value 
becomes an X'0000'. 


46 (2E) 


DCB.RTRY 


Halfword value reflecting the 
maximum number of retrys the driver 
attempts if an error occurs. 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


48 (30) 


DCB.WKEY 


Byte value reflecting any write keys 
attributed to this device. 


49 (31) 


DCB.RKEY 


Byte value reflecting any read keys 
attributed to this device. 


50 (32) 


DCB.ILVL 


Halfword value reflecting the interrupt 
level of this device. The device 
controller must be hardware wired to be 
on one of the four interrupt levels. This 
field must agree with the hardware. 


52 (34) 


DCB.ERRL 


Error logging data area pointer and 
error logging on/off switch used by the 
OS/32 Error Logging Facility. 


56(38) 


DCB.ISP 


Fullword address used as pointer to 
ISPT for this device. 


60 (3C) 


DCB.TOCH 


Fullword address pointer to next DCB 
on time-out chain only if the driver has 
put this DCB on the time-out chain. If 
this value is -1, this DCB is the last one 
on the time-out chain. 


64 (40) 


DCB.XFLG 


Halfword value reflecting specific 
information about this device. Magnetic 
tape and disk drivers use this field. 
Breakdown of this halfword value — 
Bit Meaning 

directory presence flag 

1 bit map presence flag 

2 reserved 

3 bit map modify flag 

4 reserved 

5 I/O malfunction 

6 bit map malfunction 

7 hardware protect bit 

8 restricted volume flag 

9 magnetic tape at EOV label 

10 last command to magnetic tape was 
REWIND 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 






11 magnetic tape is on or past EOT 
12-15 reserved 


66 (42) 


DCB.CLAS 


Halfword value reflecting the device 
class for OS/32 Accounting Facility 


68 (44) 


DCB.IOH 


Fullword address of the IOH list that 
the SVC1 preprocessor uses. If a user 
supplied IOH list is desired, include the 
IOH list in the device driver. 


72 (48) 




Spare 


73 (49) 


DCB.LEVL 


Byte address that specifies level for 
ADDSQ. 


74 (4A) 


DCB.IOP 


Halfword address for index of 
input/output (IOP) in APBDIR (0 for 
CPU). 


76 (4C) 


DCB.IPB 


Fullword address used as a pointer to 
input/output parameter block (IPB) for 
IOP. 


80 (50) 


DCB.SQ 


Fullword address used as a pointer to 
processor's system queue. 


84 (54) 


DCB.Q 


Fullword address of the specific queue 
strategy routine for this device. 


88 (58) 


DCB.EDMA 


Fullword address of the extended direct 
memory access (EDMA) strategy 
routine. The default routine is 
EDMACON. 


92 (5C) 




Reserved 


96 (60) 


DCB.NXT 


Fullword address of the next I/O block 
(IOB) waiting for this DCB. 


100 (64) 


DCB.RFLGS 


Halfword value reflecting various traps 
that the user wants to take upon 
completion of device driver. 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


102 (66) 


DCB.PRI 


Byte value reflecting the priority of the 
task issuing the SVC1 request. 


103 (67) 


DCB.TYPE 


Byte value defining the type of IOB 
used. 


104 (68) 


DCB.DONE 


Fullword address of a user-supplied 
routine executed at driver-termination 
time in place of the standard OS/32 
routine, IODONE. 


108 (6C) 


DCB.DCB 


Fullword address of this DCB. 


112 (70) 


DCB.TCB 


Fullword address of the task control 
block (TCB) of the task requesting the 
I/O. 


116 (74) 


DCB.QCB 


Fullword address that points to connected QCB. 


120 (78) 


DCB.ESR 


Fullword address reflecting the next 
entry point into the driver that the 
system queue service routine will 
schedule. 


124 (7C) 


DCB.UPBK 


Fullword address reflecting the logical 
address (user task relative) of the 
parameter control block within 
memory. 


128 (80) 


DCB.PBLK 


Fullword physical address of the SVC1 
parameter block. 


132 (84) 


DCB.FC 


Byte value reflecting user task 
requested function. 


133 (85) 


DCB.LU 


Byte value reflecting the logical unit 
(lu) assigned to this device. 


134 (86) 


DCB.STAT 


Byte value reflecting the device 
independent status after termination of 
the driver. 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


135 (87) 


DCB.DDPS 


Byte value reflecting the specific device 
dependent status after termination of 
the driver. 


136 (88) 


DCB.SADR 


Fullword address of the user's buffer 
starting memory location. 


140 (8C) 


DCB.EADR 


Physical address of the user's buffer 
ending memory address. 


144 (90) 


DCB.RAND 


Fullword value reflecting the user 
supplied relative record number. 


148 (94) 


DCB.LLXF 


Fullword value reflecting the length of 
data actually transferred. 


152 (98) 


DCB.SV1X 


Fullword value reflecting the specific 
communications requests or 6250 Tape 
Drive requests. 


156 (9C) 


DCB.LUE 


Fullword copy of the task's lu table 
entry. 


160 (A0) 


DCB.WCHN 


Fullword address of the TCB waiting 
for the I/O to compete for a task. 


168 (A8) 


DCB.SIZE 


Fullword value that represents the 
number of sectors on a disk; or if used 
for a vertical form control, it represents 
the number of lines on the device. 


172 (AC) 


DCB.VFC 


Fullword address of VFCDCB. 
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TABLE A-2. CHANNEL CONTROL BLOCK (CCB) 



DISPLACE- 
MENT INTO 
STRUCTURE 



LABEL 



EXPLANATION 



0(0) 



CCB.CCW 



Halfword value consisting of a status mask and byte 

value describing the channel operation to be performed. 

Breakdown of this halfword — 

Bit Meaning 

0-7 Status mask. The micro-code (ADC) 

ANDs the device status with the byte 
value contained in this field. If the result 
is zero, ADC continues with the data 
transfer. If the result is not zero, ADC 
vectors to the halfword address contained 
in CCB.SUBA and the condition code is 
set to XT. 

8 Execute bit. If this bit is reset, ADC 
vectors to the halfword value contained in 
CCB.SUBA and the condition code is set 
to X*0\ If this bit is set, ADC continues 
with the data transfer. 

9 Reserved. 

10-11 Redundancy check bit. This byte specifies 
the type of redundancy checking required. 
Break down of this bit — 
Bit 10 Bit 11 



1 

1 
1 1 

12 Buffer select switch. If this bit is reset, 
buffer is used. If this bit is set, buffer 1 
is used. 

13 Read/write bit. If this bit is reset, a byte is 
read from the device to the processor. If 
set, a byte is written from the processor to 
the device. 



Meaning 
LRC 

BISYNC CRC 
reserved 
SDLC CRC 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 






14 Translation bit. If this bit is reset, 
translation does not occur. A 'TLATE' 
instruction is not required; but, the driver 
defined translation table is set as is for this 
instruction. Reference the Processor 
User's Manual. 

15 Fast bit. If this bit is set, the fast data 
transfer mode occcurs--only buffer is 
used; translation and redundancy checking 
do not occur. This bit must be set for 
halfword devices. 


2(2) 


CCB.LBO 


Halfword value reflecting the negative length of buffer 
0. ADC adds one to this field and transfers a data byte 
until this value turns positive (not zero). When this value 
turns positive, ADC compliments the buffer select switch 
(if fast bit is reset), vectors to the halfword address 
contained in CCB.SUBA, and sets the condition code to 
X'2\ 


4(4) 


CCB.EBO 


Fullword ending address of the driver's buffer 0. 
Typically, the driver places this address contained in 
DCB.EADR into this field. To determine what byte to 
transfer, ADC adds the contents of CCB.LBO to 
CCB.EBO. 


8(8) 


CCB.CW 


Byte value containing the accumulated value of either 
cyclic or longitudinal redundancy checking. The initial 
value of this field is zero. 


10 (A) 


CCB.LB1 


Halfword value reflecting the negative value of buffer 1. 
Reference the description of CCB.LBO. 


12 (C) 


CCB.EB1 


Fullword ending address of the driver's buffer 1. Most 
drivers use this field to point to control characters to be 
sent to the device after LBO goes positive. 


16 (10) 


CCB.XLT 


Fullword address of a driver defined translation table. 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


20 (14) 


CCB.SUBA 


Halfword address of a driver's interrupt service routine 
(ISR). The address contained in this field is vectored to 
if — 

-upon device interrupt, the execute 
bit within the CCB.CCW is reset, 
-LB0 or LB1 goes positive, or 
-bad status is received from the device. 


22 (16) 


CCB.MISC 


Driver defined. 


23 (17) 


CCB.FLGS 


Driver defined. 


24 (18) 


CCB.DCB 


Fullword address of the DCB assigned for this data 
transfer or command function. 


storage 


CCB.DVDP 


End of device-independent segment. 


28 (1C) 


CCB.XLT2 


Fullword address for secondary translate table. 
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TABLE A-3. INPUT/OUTPUT (I/O) BLOCK 



DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


0(0) 


IOB.NXT 


Fullword address of next IOB on IOB 
chain. If this field contains zero, this 
IOB is the last on the chain. 


4(4) 


IOB.RFLG 


Halfword value reflecting request 
dependent conditions and caller task 
states. Breakdown of this halfword — 
Bit Meaning 

connection completed 

1 caller in I/O wait 

2 caller expects an I/O trap 

3 caller in connection wait 

4 ISPT reset flag, 1 equals no reset 

5 EDMA exclusive request 

6 EDMA connected flag 

7 no disconnection at I/O completion 

8 system I/O 

9 no purge on error 

10 request cannot be halted 

11 wait pending request 

12 reserved 

13 do not free IOB at connect time 

14 vertical forms control flag 


6(6) 


IOB.PRI 


Byte value reflecting the dispatch 
priority of the requesting task. 


7(7) 


IOB.TYPE 


Byte value defining the type of IOB. 
possible values and appropriate 
meanings. 
Value Meaning 

1 in TCB pool; reserved at LINK time 

2 spare TCB (one per each task) 

3 contained in parameter control 
block (PCB) 

4 contained in contiguous file's DCB 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


8(8) 


IOB.DONE 


Fullword address of driver defined 
IODONE routine. If this field contains 
a zero, IODONE is executed. 


12(C) 


IOB.DCB 


Fullword address of the DCB for this 
request. 


16 (10) 


IOB.TCB 


Fullword address of the TCB for this 
request. 


20 (14) 


IOB.QCB 


Fullword address pointing to QCB for 
this IOB 


24 (18) 


IOB.ESR 


Fullword address reflecting the entry 
into the driver's initialization ESR or 
termination ESR. System queue service 
(SQS) schedules both for execution. 


28 (1C) 


IOB.UPBK 


Fullword unrelocated (logical) address 
of requester's PCB. 


32 (20) 


IOB.PBLK 


Fullword relocated (physical) address 
of requester's PCB. 


33 (21) 


IOB.FC 


Byte value reflecting requester's 
function code. 


34 (22) 


IOB.LU 


Byte value reflecting requester's 
assigned lu. 


35 (23) 


IOB.STAT 


Byte value reflecting the device- 
independent status. 


36 (24) 


IOB.DDPS 


Byte value reflecting the device- 
dependent status. 


40 (28) 


IOB.SADR 


Fullword starting address of the user's 
buffer. 


44 (2C) 


IOB.EADR 


Fullword ending address of the user's 
buffer 


48 (30) 


IOB.RAND 


Fullword value reflecting the relative 
record number if the request is for 
indexed file. 
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DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


52 (34) 


IOB.LFX 


Fullword value for length of transfer. 


56 (38) 


IOB.SV1X 


Extended SVC1 fullword. 


60 (3C) 


IOB.LUE 


Fullword copy of lu table entry of task. 
Reference DCB.LUE. 


64 (40) 


IOB.WCHN 


Fullword address of a TCB waiting for 
the I/O for this task to complete. 


68 (44) 


IOB.CYL 


Halfword value for cylinder *2 for disk 
access. 


70 (46) 


IOB.SECT 


Byte value for relative sector on disk 
for seek. 


71 (47) 


IOB.LSEC 


Byte value for last relative sector used 
for seek. 
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TABLE A-4. EVENT COORDINATION NODE 



DISPLACE- 
MENT INTO 
STRUCTURE 


LABEL 


EXPLANATION 


0(0) 


EVN.CORD 


Upper pointer 


4(4) 


EVN.FLGS 


Flags - must match QCB.FLGS 


6(6) 


EVN.LOCK 


T & S lock for multiprocessing 


8(8) 




Spare 


9(9) 


EVN.CLEV 


Connection level 


10(A) 


EVN.TSIZ 


Tree size 


14(E) 


EVN.SQS 


SQS executor 


18 (12) 


EVN.DCB 


DCB address 


22 (16) 


EVN.TCB 


TCB address 


26 (1A) 


EVN.QCB 


Pointer to current QCB 


30 (IE) 


EVN.EVRS 


Save area for EVREL 


32 (20) 


EVN.NIO 


Count of I/O's (connected + queued) 


34 (22) 


EVN.HWIO 


HWM of EVN.NIO 


38 (26) 


EVN.CLC 


Connected leaf chain 


42 (2A) 


EVN.PREV 


Previous (node) pointer 


46 (2E) 


EVN.NEXT 


Next (node) pointer 


50 (32) 


EVN.TOP 


Top of waiting queue 


54 (36) 


EVN.BOT 


Bottom of waiting queue 


56 (38) 


EVN.CYL 


Current cylinder position 


57 (39) 


EVN.RDCT 


Redispatch count 


58 (3 A) 




Reserved 


38 (26) 


EVN.EMAX 


EQU EVN.CLC - EDMA max transfers value 


40 (28) 


EVN.ECTR 


EQU EVN.CLC + 2 - EDMA active transfer value 


38 (26) 


EVN.WRAP 


EQU EVN.CLC - disk leaf secondary queue pointer 



A -14 
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APPENDIX B 

MACHINE STATES 

Event Service (ES) State 

• Used by: 

— System Queue Service (SQS) 

— Device Driver Events (initialization and termination 

— System events (clocks, power restore) 

• Nontask State: 

— SQS Interrupts Disabled 

— No Context Block 

— SVCs are Illegal 

• Register Set 5, if available, else set F. 

• Entered via: 

— System Queue "Interrupt" 

— LPSW from Task Dispatcher 

. Exits via: LPSW to Task Dispatcher 

• This state uses register thru 15 of set 5. The data input registers (DIRs) and intermediate 
event service routine (ESRs) and termination ESRs of drivers are executed in this state. 



Nonreentrant System (NS) State 



• Used by: 

— First Level Interrupt Handlers (Faults and service calls (SVCs)) 

— Short SVC Second Level interrupt handlers 

— Task Dispatcher 

• Nontask State: 

— SQS Interrupts Disabled 

— No Context Block 

— SVCs are Illegal 

• Register Set 

(Restricted to Registers 8-F) 
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• Entered Only Via: 

— Internal Interrupt (Fault or SVC) 

— Call to Dispatcher (LPSW) 

• Exit Via: 

— TMNSOUT: Return to current task 

— TMDISP: Dispatcher 

— TMRS(A)IN: Enter RS(A) state 

• All SVC and fault handlers execute in this state initially. Certain SVC and fault handlers may 
switch to another state. With respect to drivers, NS state is used by SVC1 and input/output 
handlers (IOH). 

User Task (UT) State 



• Tasklevel States: 

— Use "User" Context Block at TCB.UT 

— SQS Enabled 

— SVCs are Legal 

. UT State PSW: 

— Relocation/Protection Enabled 

— Privileged Instruction Illegal 

• Entered via: 

— Task Dispatcher 

— TMNSOUT 

• Exit via: 

— Interrupt (SVC or Fault) 

• Uses registers through 15 of set 15. 

• User programs, e-tasks, d-tasks, the operation system (OS) command processor, console monitor 
and loader execute in this state. Drivers do not execute in this state. 

Interrupt Service (IS) State 

• Uses registers through 7 of set for level 0. For levels 1 through 3, the IS state uses register 
through 15 of sets 1 through 3, respectively. 

• The interrupt service routines (ISRs) of drivers execute in this state. 
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Reentrant System (RS) State 



• Uses registers through 15 of set 6. 

• Certain SVCs, fault handlers and file managers execute in this state. Drivers do not use this 
state. 

Figure B-l depicts the various machine states and their associated registers and register sets. 

190-4 



REGISTERS 

1 





SETS 



1 



□ 



NS = j I SVC INTERRUPT HANDLERS AND I/O HANDLER ROUTINES 
IS = vZZ\ INTERRUPT SERVICE ROUTINES 



ES 



RS = 



UT = 



ALL I/O DRIVEN CODE, EXCEPT INTERRUPT SERVICE 
PRIMARILY FILE MANAGER CODE 
USER TASKS 



Figure B-l. Machine States and Associated Registers and Registers Sets 
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Figure B-2 depicts driver machine states and the driver routines, in sequence, that are associated 
with them . 



IDH 



DIR ISR1 ESRn ISRn TERM 



IOOONE 




Figure B-2 Machine States and Associated Driver Routines 
In their Proper Time Sequence 
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Where: 

SQ is scheduled by adding the leaf for the device to the system queue. 

INT is scheduled by executing a SINT instruction or by an interrupt from a device. 
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APPENDIX C 
OS/32 MACROS 

THE SYSGEN/32 MACRO OUTPUT FILE 

NOTE 

For the SYSGEN/32 macro input file, see Chapter 7. 



IMPUR 

MCALL DCBI , CCBI , CONVNUM, EVNGEN, $TABL$ 

MCALL BI0CGEN,DCB39 

MCALL MTPI,DCB64 

MCALL DCB246 

SPTINIT MLBL=120,CSLV=5,CSBF=122,ISPT=500,MTOP=2048,NTCB=51, C 

SVOL=OS32,RVOL=FIXD,TVOL=FIXD,FREQ=60,PIC=6C,LFC=6D, C 

CPU=3230,SLICE=200,SPVL=FIXD,VERSN=0S32LAB,CLASS=4, C 

SOPT=92F67000, ERBL=X 
DMT CON , LABI , LAB2 , CRT1 , CRT2 , PRT , PR , MAGO , MAGI , DSC1 
DMT DSC2 
DMTEND 
SPDMT PR 
DCBINIT 
DCB39 DCOD=39,DN=16,NAME=CON,CONS=l,ILVL=0,XDCD=X , 280D\ C 

RECLN=120 
DCB39 DCOD=39 . DN=18 , NAME=CRT1 , I LVL=0 , XDCD=X ' 280D ' 
DCB39 DCOD=39,DN=20,NAME=CRT2, ILVL=0, XDCD=X' 280D ' 
DCB113 DCOD=113,DN=98,NAME=PRT, ILVL=0 
DCBI DC0D=1 , DN=0 , NAME=PR , I LVL=0 , XDCD=X ' 71 ' 
DCB64 DC0D=64, DN=133 , NAME=MAGO, ILVL=0, SLCH=FO, CNTR=1 
DCB64 DC0D=64, DN=197, NAME=MAG1, ILVL=0 / SLCH=F4, CNTR=2 
DCB51 DC0D=51 , DN=198 , NAME=DSC1 , ILVL=0 , SLCH=FO , CNTR=B6 
DCB50 DC0D=50 , DN=199 , NAME=DSC2 , ILVL=0 , SLCH=FO , CNTR=B6 , C 

SHCCB=DSC1 
DCBTERM 
DCB246 COUNT=10, DC0D=246 , DN=208 , NAME^LABl , ILVL=0 
DCB246 DC0D=246 / DN=216, NAME=LAB2 , ILVL=0 
VMTGEN 2 
EVNGEN DCOD=39 , NAME=CON , TS I Z=l , NUM=0 
EVNGEN DCOD=246 , NAME=LAB1 , TSIZ=1 , NUM=0 
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EVNGEN DC0D=246 , NAME=LAB2 , TSI Z=l , NUM=1 

EVNGEN DC0D=39 , NAME=CRT1 , TSI Z=l , NUM=1 

EVNGEN DC0D=39 , NAME=CRT2 , TSI Z=l , NUM=2 

EVNGEN DC0D=113 , NAME=PRT , TSI Z=l , NUM=0 

EVNGEN DC0D=64 , NAME=MAGO , TSI Z=3 , NUM=0 , TYP1=C , C00RD=1 , UN0D=1 

EVNGEN DC0D=64 , NAME=MAG1 , TS I Z=3 , NUM=1 , TYP1=C , C00RD=2 , UN0D=1 

EVNGEN DC0D=51 , NAME=DSC1 , TS I Z=3 , NUM=0 , TYP1=C , C00RD=B6 , UN0D=1 , C 

DA=1 
EVNGEN DC0D=50 , NAME=DSC2 , TSI Z=3 , NUM=0 , TYP1=C , C00RD=B6 , UN0D=1 , C 

DA=1 , BITDIR=1 , LAST=1 , ERBL=1 , CPU=32 30 
EVNGEN DC0D=1,NAME=C,TSIZ=0,NUM=0 / TYP1=S,C00RD=F0,UN0D=1, C 

TYP=C,ELGS=0 
EVNGEN DC0D=2,NAME=C,TSIZ=0,NUM=0,TYP1=S,C00RD=F4,UN0D=1, C 

TYP=C,FLGS=0 
EVNGEN DCOD=B6,NAME=C,TSIZ=0,NUM=O / TYPl=S,C00RD=FO,UNOD=l, C 

TYP=C,ELGS=0 
EVNGEN DC0D=F0 , NAME=S , TSI Z=0 , NUM=0 , TYP=S , FLGS=0 
EVNGEN DC0D=F4 , NAME=S , TS I Z=0 , NUM=0 , TYP=S , FLGS=0 

FLTPINIT U=0,CPU=3230,REGS=8 

EXTRN UB0T.F01 

EXTRN CDVR.F01 

EXTRN CMDB.F33 

EXTRN CMEX.F33 

EXTRN CMON . F01 

EXTRN CMSP.F33 

EXTRN CMIR.F02 

EXTRN ERRC.F03 

EXTRN EXAC.F02 

EXTRN EXIN.F53 

EXTRN EXI0.F02 

EXTRN EXLD.F53 

EXTRN EXMY.F53 

EXTRN EXSP.F53 

EXTRN EXSV.F53 

EXTRN EXTI.F01 

EXTRN EXTM.F53 

EXTRN FMCO.F33 

EXTRN FMIN.F33 

EXTRN FMS7.F33 

EXTRN FMA7.F33 

EXTRN FMB7.F33 

EXTRN FMUT.F33 

EXTRN INTC.F02 
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EXTRN ITEM. MOO 
EXTRN MCHK.F02 
EXTRN APSV.FOl 
IVTGEN CSL='CON' , MXBX=32000, MXPRI=10, SYSS=204800, C 

ERFD= * 0S32ERR0R LOG ' , ERDS=200 , ERDP=2 , PWRDLAY=0 , C 

PWRMODE=MANUAL 
SVTGEN MBLK=100,DBLK=5, IBLK=1,DSPL=5, ISPL=1, DNBF=64, INBF=3 
DELIST 15, SQ 

SMCONFIG BLOCK=0, START=0,RANGE=2 / INTERL=0 
STARTUP 
END 



THE DEVICE CODE::: MACRO 

NOTE 

This device control block (DCB) is extracted from 
DCBFORM in the SYSGEN/32 macro library. 

MACRO col 72 

DCB : : : %DCOD= , %DN= , %CLAS= , %I LVL= , %NAME= , %QU= , 1 

%CONS= , %SLCH= , %CNTR= , %XDCD= , %SPND= . 2 

%RECLN= , %SPCR= , %SPCW= , %XLT= , %PDCT= , %LDCT= , 3 

%SHCCB=, %POLMT=, %EOV=0 , %CLOCK=, %SIZE=, %DUAL=, 4 

%SCR=, %RES=%CM=, %ITV=, %IOLM=, %SLS=, %MNOF=, %MBFS= / 5 

%MRBS= , %MTO= , %N2= , %NC= , %OTV= , %PLDT= , %PLTC= , %SSA= , 6 
%T1=, %UCSI=, %UCSO=, %WKTC= 

DEFINE GLOBAL COUNTER FOR DEVICE CODES 

GBLC %IDVAL DECLARE DEVICE ALPHA GLOBAL VARIABLE 

BGBLA %ID::: DECLARE DEVICE GLOBAL VARIABLE 

LCLA %CCBFL LOCAL VARIABLES AS NEEDED 

LCLA %CLASN 

LCLC %RXLT,%RQU 

LCLC %CORDNM / %PTRPAS 

LCLC %OFFS 
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LCLA %RDN 

LCLC %MDN , %MCNT , %MSLCH 

LCLA %TRCNT,%UPTR 

LCLB %FOUND,%DA 

BGBLA %FIRST 
%RQU SETC 'COMQ' DEFAULT DEVICE QHANDLER 

%MDN SETC '%DN' DEVICE ADDRESS 

%MCNT SETC '^CNTR' CONTROLLER 

%MSLCH SETC '%SLCH' SELCH 

%CCBFL SETA 

AIF (T'%CLAS EQ 'U')&CLSNTD 
%CLASN SETA %CLAS*12 I0CLASS*12 

&CLSNTD ANOP 

MACRO CALL TO 

USERINIT INITIALIZE STRUC COPY FLAGS 

CONVNUM VAL=%ID::: CONVERT %ID: : : TO ALPHA 

%IDVAL RETURNED WITH ALPHA 
VALUE OF %ID: : : 
%ID::: SETA %ID:::+1 BUMP UP FOR NEXT TIME 



DCB%NAME PROG DCB PROGRAM LABEL FOR LINK MAP 



&DCBOPT ANOP 



Now replace all values passed in the macro call. 

%OFFS SETC '%DCOD' : ^IDVAL' ESTABLISH PROPER OFFSET 

(The label %DCB:%DCOD:%IDVAL is established as the start address of the DCB in DCBI.) 
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The following is a sample of how some of the passed parameters may be handled. 

DEFINE SYSTEM DEPENDANT FIELDS OF DCB FIRST 

ORG DCB%OFFS+DCB.DN DEVICE ADDRESS 
DC H ' %DN ' 

A separate leaf is created unless the %SHCCB parameter is passed. If it is passed, it will contain 
the name of the shared busy device. The leaf is created by the EVNGEN macro (see the 
SYSGEN/32 Macro Output file above). 



&NSLEAF 



&NRMLFX 
&NOLEAF 



ORG DCB%OFFS+DCB.LEAF LEAF POINTER 

AIF (T^SHCCB' EQ ' U ' ) &NSLEAF B IF NOT SHARED 

DAC LF%SHCCB USE SHARED DEVICE LEAF 

EXTRN LF%SHCCB 

AGO &NRMLFX 

ANOP 

DAC LF%OFFS GENERATE STANDARD LEAF NAME 

EXTRN LF%OFFS 

ANOP 

ANOP 



DEFINE ALTERNATE NAME FOR DMT MACRO 
DCB_%NAME EQU DCB%OFFS 
ENTRY DCB_%NAME 
ORG DCB%OFFS+DCB.DMT 
DC DMT_%NAME A (DMT ENTRY) 
EXTRN DMT_%NAME 



&NOCLAS 



AIF 
ORG 
DC 
ANOP 



(T'%CLAS EQ 'U'J&NOCLAS 
DCB%OFFS+DCB . CLAS 
H'%CLASN' 



10 CLASS 
I0CLASS12 



&N0ILVL 



AIF 
ORG 
DC 
ANOP 



(T'%ILVL EQ 'U')&NOILVL 
DCB%OFFS+DCB.ILVL ILEVEL 
H'%ILVL' 
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CONTINUE WITH OTHER DCB OPTIONS (DEVICE -DEPENDENT) 



&NOXDCD 



AIE (T*%XDCD EQ 'U')&NOXDCD IF NOT ENTERED 

ORG DCB%OFFS+DCB.XDCD ELSE MOVE XDCD 

DC %XDCD EXTENDED DCOD 

ANOP 



&NOSLCH 



AIF (T'%SLCH EQ 'U')&NOSLCH 

ORG DCB%OFFS+DCB.SDN SELCH 

DCX %SLCH ' 

ANOP 



&NOCNTR 


ANOP 




AIF 




ORG 




DC 




DC 


&NOSPND 


ANOP 



AIE (T'%CNTR EQ 'U')&NOCNTR 

ORG DCB%OFFS+DCB.CDN CONTROLLER 

DCX %CNTR 



(T'%SPND EQ 'U*)&NOSPND 
DCB%OFFS+DCB . XDCD 

H'%SPND' FLOPPY SPINDLE 

H'O' 



AIF (T'%QU EQ 'U')&DEFQU 
ORG DCB%OFFS+DCB.Q 10 QUEUING 
DAC %QU 
EXTRN %QU 
AGO &NOQU 
&DEFQU ANOP 



&NOQU 



AIF ('%RQU* EQ ")&NOQU 
ORG DCB%OFFS+DCB.Q 
DAC %RQU 
EXTRN %RQU 
ANOP 



AIF 
ORG 
DC 
&NOCLOCK ANOP 



(T'%CLOCK EQ 'U')&NOCLOCK 
DCB%OFFS+DCB . CCB+6 
%CLOCK DEFINE CLOCK 



AIF 
ORG 



(T'%RECLN EQ 'U')&NORECLN 



DCB%OFFS+DCB.RECL 



RECORD SIZE 
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DC H'%RECLN' 
&NORECLN ANOP 

AIF (T'%SPCR EQ 'U')&NOSPCR 

ORG DCB%OFFS+DCB.SPCR 

DC %SPCR SPECIAL READ CHARACTER 

&NOSPCR ANOP 

AIF (T'%SPCW EQ 'U')&NOSPCW 

ORG DCB%OFFS+DCB . SPCW 

DC %SPCW SPECIAL WRITE CHARACTER 

&NOSPCW ANOP 

AIF (T'%SCR EQ *U')&NOSCR 

ORG DCB%OFFS+DCB.T01 

DC %SCR SCREEN TRANSMIT TIME 

&NOSCR ANOP 

AIF (T'%RES EQ 'U')&NORES 

ORG DCB%OFFS+DCB.T02 

DC %RES RESPONSE TIME 

&NORES ANOP 

AIF (T'%XLT EQ 'U')&DEFXLT 

ORG DCB%OFFS+DCB.XLT 

DAC %XLT TRANSLATION TABLE 

EXTRN %XLT AND EXTRN 

AGO &NOXLT 
&DEFXLT ANOP 

AIF ( ' %RXLT ' EQ " ) &NOXLT 

ORG DCB%OFFS+DCB.XLT TRANSLATION TABLE 

DAC %RXLT 

EXTRN %RXLT AND EXTERN 

&NOXLT ANOP 

AIF (T'%LDCT EQ 'U*)&NOLDCT 

ORG DCB%OFFS+DCB.LDCT 

DC H'%LDCT' LEAD. CHAR. COUNT 

&NOLDCT ANOP 

AIF (T'%PDCT EQ ' U ' ) &NOPDCT 

ORG DCB%OFFS+DCB.PDCT 
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DC H'%PDCT' 
&NOPDCT ANOP 



PAD COUNT 



AIF (T'%POLMT' EQ 'U')&NOMXEC 

ORG DCB%OFFS+DCB.MXEC 

DC %POLMT MAX POLL ERR RETRY- POLL LIMIT 

&NOMXEC ANOP 

AIF (T'%DUAL' EQ 'U'J&NODUAL 

ORG DCB%OFFS+DCB.DUAL DUAL PORT OPTION 

DC X ' FF ' 
&NODUAL ANOP 



ORG $ST%OFFS 
%RDN SETA %DN+1 
USEREND 
MEND 



ORG TO END OF DCB 



MUST END THIS SOURCE MODULE 



MEND 



THE DCBI MACRO 



MACRO 
%SYM DCBI 



%DCOD= , %I NI T= , %TERM= , %TOUT=7FFF , %DA= , %I OC=0 , 

%I OH=COMI OH , %EDMA=0 , %COPY=$DCB$ , 

%FUNC=0 , %ATRB=0 , %RECL=0 , %SI ZE=DCB . DVDP+4 , 
%FLGS=DFLG.LNM, %ID=, %DSIZE=, %STRK=, %TCYL=, 

%BMSA= , %DRSA= , %DSC= , %NUM= . %SADR= , %SHCC=0 , 

%CC4=, %CLOC= / %CCB=, 

%PFUN= , %PXLT= , %RXLT= , 



1 
2 
3 
4 
5 
6 
7 
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%PSEP=, %EOLC=, %RTRY= 
LCLA %IOCLN 

%IOCLN SETA %I0C*12 IOCLASS * 12 

TITLE DCB%DCOD%ID 

IMPUR 

ENTRY DCB%DCOD%ID 

AIF ('%INIT' EQ '0*)&NOINIT 

EXTRN %INIT 
&NOINIT ANOP 

AIF ('%TERM' EQ '0')&NOTERM 

EXTRN %TERM 
&NOTERM ANOP 

EXTRN %IOH 

%COPY 
D%SYSINDX EQU * 
DCB%DCOD%ID EQU * 

NLIST 

DO %SIZE/4 

DAC 

LIST 
$ST%DCOD%ID EQU * MARK END OF DCB 

AIF (T'%EDMA EQ 'U')&NEDMA 

ORG D%SYSINDX+DCB.EDMA 

DAC %EDMA DEFINE EDMA 

AIF (^EDMA' EQ '0')&NEDMA 

EXTRN %EDMA 
&NEDMA ANOP 

ORG D%S YS I NDX + DCB . I N I T 

DAC %INIT DRIVER I NIT 

AIF C%FUNC' EQ '0')&NOEXT 



EXTRN %FUNC 

&NOEXT ORG D%SYSINDX+DCB.FUNC 

DAC %FUNC 

ORG D%SYSINDX+DCB.TERM 

DAC %TERM 

ORG D%SYSINDX+DCB.ATRB 

DCX %ATRB 

ORG D%SYSINDX+DCB.CLAS 

DC H*%IOCLN' 

ORG D%SYSINDX+DCB.RECL 

DC H ' %RECL * 

ORG D%SYSINDX+DCB.TOUT 



DRIVER FUNCTION ROUTINE 

DRIVER TERMINATION 
DEVICE ATTRIBUTES 

10 CLASS 
RECORD LENGTH 
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DCX 




ORG 




DAC 




ORG 




DB 




ORG 




DAC 




ORG 




DAC 




AIF 




ORG 




DAC 




EXTRN 


&NSADR 


ANOP 




AIF 




ORG 




DAC 




EXTRN 




ORG 




DAC 




EXTRN 


&NODA 


ANOP 




AIF 




ORG 




DB 


&NCC4 


ANOP 




AIF 




ORG 




DCX 


&NCLOC 


ANOP 




AIF 




ORG 




DC 




ORG 




DC 




ORG 




DC 


&NDSIZE 


ANOP 




AIF 




ORG 




DC 




DC 


&NBMSA 


ANOP 



%TOUT TIME-OUT CONSTANT 

D%SYSINDX+DCB . FLGS 
%FLGS DEVICE FLAGS 

D%SYSINDX+DCB.DCOD 
%DCOD DEVICE CODE 

D%SYSINDX+DCB. IOH 
%IOH 10 HANDLER 

D%S YS I NDX + DCB . DCB 
D%SYSINDX DCB ADDRESS 

(T'%SADR EQ *U')&NSADR 
D%SYSINDX+DCB . SADR 
%SADR SADR 

%SADR 

(T'%DA EQ 'U')&NODA 

D%SYSINDX+DCB.DIRL POINT TO DIR.LEAF 
DIR%DCOD%ID IF DIR. ACCESS 
DIR%DCOD%ID 
D%SYSINDX+DCB.BITL 
BIT%DCOD%ID BIT. LEAF ALSO 
BIT%DCOD%ID 

(T'%CC4 EQ 'U')&NCC4 
D%SYSINDX+DCB.CCB+4 
X ' %CC4 ' , 

(T'%CLOC EQ 'U')&NCLOC 
D%SYSINDX+DCB.CCB+6 
%CLOC CLOCK SPEC. 

(T'%DSIZE EQ 'U')&NDSIZE 
D%SYSINDX+DCB.SIZE 
%DSIZE DISC SIZE 

D%SYSINDX+DCB . STRK 

X ' %STRK ' SECTORS/TRACK 

D%SYSINDX+DCB.TCYL 
X ' %TCYL ' TRACKS/CYL 

(T'%BMSA EQ 'U'J&NBMSA 
D%SYSINDX+DCB.BMSA BITMAP BUFFER 
D%SYSINDX+DCB. :%BMSA 
D%SYSINDX+DCB. :%BMSA+255 
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&NDRSA 



&NDSC 



&NNUM 



&NPFUN 



&NPXLT 



&NRXLT 



&NPSEP 



&NEOLC 



&NRTRY 



AIF 

ORG 

DC 

DC 

ANOP 

AIF 

ORG 

DC 

EXTRN 

ANOP 

AIF 

ORG 

DC 

ANOP 

AIF 

ORG 

DC 

ANOP 

AIF 

ORG 

DAC 

EXTRN 

ANOP 

AIF 

ORG 

DAC 

EXTRN 

ANOP 

AIF 

ORG 

DC 

ANOP 

AIF 

ORG 

DCX 

DCX 

ANOP 

AIE 

ORG 

DCX 

ANOP 

AIF 

ORG 



(T'%DRSA EQ 'U')&NDRSA 
D%SYSINDX+DCB.DRSA DIR. BUFFER 
D%SYSINDX+DCB. :%DRSA 
D%SYSINDX+DCB. :%DRSA+255 

(T'%DSC EQ *U')&NDSC 
D%SYSINDX+DCB.DSC 
%DSC DSC 

%DSC 

(T'%NUM EQ 'U')&NNUM 
D%SYSINDX+DCB.NUM 
X ' %NUM ' NUM 

(T'%PFUN EQ 'U')&NPFUN 
D%SYSINDX+DCB.PFUN 
H ' %PFUN ' PFUN 

(T'%PXLT EQ *U')&NPXLT 

D%SYSINDX+DCB.PXLT FOR CARD RDR PUNCH 
%PXLT PUNCH TRANSATION 

%PXLT 

(T'%RXLT EQ 'U'J&NRXLT 
D%SYSINDX+DCB.RXLT 



%RXLT 
%RXLT 



FOR CARD RDR PUNCH. 
READ TRANSLATION 



(T'%PSEP EQ 'U')&NPSEP 

D%SYSINDX+DCB.PSEP FOR CARD RDR PUNCH 
X'%PSEP' PUNCH SEPARATE 

(T'%EOLC EQ 'U')&NEOLC 
D%SYSINDX+DCB . EOLC 
%EOLC(l) PRINTER EOLC 

%EOLC(2) 

(T'%RTRY EQ 'U'J&NRTRY 
D%SYSINDX+DCB . RTRY 
%RTRY RETRY 

(*%SHCC' NE 'O'J&NOCCBX IF NOT DONT DO DCB . CCB 
D%SYSINDX+DCB.CCB DCB. CCB 
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C-ll 



AIF (T'%CCB EQ 'U')&NOCCBX 

DC Z (CCX%DCOD%ID) GENERATE SECOND CCB 
&NOCCBX ANOP 

ORG $ST%DCOD%ID BACK TO END OF DCB 
MEND 



THE CCBI MACRO 



MACRO 
%SYM CCBI %DCOD= , %XLTAB= , %SUBA= , %EBO= , 
%CCW=, %CFLGS=, %ID=, %CCBN= 

$CCB 

PURE 

AIF (T'%CCBN NE 'U'J&CCBNX 2ND CCB BRANCH 

TITLE CCB%DCOD%ID DEFINE FOR 1ST CCB 

ENTRY CCB%DCOD%ID 
CCB%DCOD%ID EQU * 

AGO &CCBN5 
&CCBNX ANOP 

TITLE CCX%DCOD%ID 

ENTRY CCX%DCOD%ID 
CCX%DCOD%ID EQU * 
&CCBN5 ANOP 
C%SYSINDX EQU * 

DO CCB+3/4 

DAC 

AIF (T'%CCBN EQ 'U')&CCBN7 B IF FIRST CCB 
$SX%DCOD%ID EQU * LABEL FOR 2ND CCB 

AGO &CCBN9 
&CCBN7 ANOP 
$S%DCOD%ID EQU * MARK END OF CCB 



B OVER 2ND CCB I NIT. 
DEFINE FOR 2ND CCB 



CLEAR CCB AREA 
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&CCBN9 



&NOXLTAB 



&NOSUBA 



&NOCCW 



&NOCFLGS 



&NOEBO 



&DONE 



ANOP 

ORG 

DAC 

AIF 

ORG 

DAC 

EXTRN 

ANOP 

AIF 

ORG 

DC 

EXTRN 

ANOP 

AIF 

ORG 

DC 

ANOP 

AIF 

ORG 

DB 

ANOP 

AIF 

ORG 

DC 

ANOP 

ORG 

AIF 

ORG 

ANOP 

MEND 



C%SYSINDX+CCB.DCB CCB.DCB 
DCB%DCOD%ID 

(T*%XLTAB EQ 'U'J&NOXLTAB 
C%SYSINDX+CCB.XLT TRANSLATE TABLE 
%XLTAB 
%XLTAB 

(T'%SUBA EQ 'U')&NOSUBA 
C%SYSINDX+CCB.SUBA CCB.SUBA 
Z (%SUBA) 
Z (%SUBA) 

(T'%CCW EQ 'U')&NOCCW 
C%SYSINDX+CCB.CCW CCB.CCW 
X ' %CCW ' 

(T'%CFLGS EQ 'U')&NOCFLGS 
C%SYSINDX+CCB.FLGS CCB.FLGS 
X ' %CFLGS ' 

(T'%EBO EQ 'U')&NOEBO 
C%SYSINDX+CCB.EBO CCB.EBO 
Y'%EBO" 



$S%DCOD%ID 



ORG TO END OF CCB 



(T'%CCBN EQ 'U')&DONE 
$SX%DCOD%ID 



ORG TO END OF SECOND CCB 
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THE USERINIT MACRO 



MACRO 

USERINIT 

GBLB %CCB, %PDCB, %DFLG, %SDCB, %VFCDCB 

%DCB$ , %DDCB , %MMDDX , %DDEX 

%MTP , %BI OCDCB , %LPTDCB , %CDRP 

%ICCB, %IDCB, %ODCB / %S125DCB, %BDCB , %ADCB , %AOBDCB 

%ETHDCBS , %ETHSTCM 

%E VN , %I OB$ , %I OB , %RCTX , %TCB 



%CCB 

%PDCB 

%DFLG 

%SDCB 

%VFCDCB 

%DCB$ 

%DDCB 

%MMDDX 

%DDEX 

%MTP 

%BI OCDCB 

%LPTDCB 

%CDRP 

%ICCB 

%IDCB 

%ODCB 

%S125DCB 

%BDCB 

%ADCB 

%AOBDCB 

%ETHDCBS 



GBLB 
GBLB 
GBLB 
GBLB 
GBLB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 
SETB 


















o 






o 





$CCB - CHANNEL CONTROL BLOCK 

$PDCB - DEVICE INDEPENDENT DCB 

$DFLG - DCB FLAGS 

$SDCB - SPOOL DCB 

$VFCDCB - VFC DCB 

$DCB$ - DISK DCB 

$DDCB - DISK DEPENDENT DCB 

$MMDDX - MMD DISK DCB 

$DDEX - ERROR LOGGER DATA AREA 

$MTP - MAG TAPE DCB 

$BI OCDCB - BIOC CRT DCB 

$LPTDCB - LINE PRINTER DCB 

$CDRP - CARD READER/PUNCH DCB 

$ICCB - DATA COMM CCB 

$IDCB - BASIC DATA COMM DCB 

$ODCB - PE 1200 DCB 

$S12SDCB - PE 1250 DCB 

$BDCB - BISYNC DCB 

$ADCB - ASYNC DCB 

$AOBDCB - DATA COMM DCB 

$ETHDCBS - ETHERNET DCB 
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%ETHSTCM 


SETB 





%EVN 


SETB 





%IOB$ 


SETB 





%IOB 


SETB 





%RCTX 


SETB 





%TCB 


SETB 
MEND 






$ETHSTCM - ETHERNET DCB 

$EVN - LEAF/NODE 

$IOB$ - I/O BLOCK & FLAGS 

$IOB - I/O BLOCK 

$RCTX - RSA CONTEXT BLOCK 

$TCB - TASK CONTROL BLOCK 



THE USEREND MACRO 



MACRO 

USEREND 

ASIS 

END 

MEND 



MUST END THIS MODULE 



ISPMOD 



IOP MACROS 



%LABEL 



ISPMOD 

EPSR 

TI 

BZ 

SLLS 

L 

ST 

SRLS 

B 



%I TEM= , %DCB= , %DN= , %WORK= 

%WORK(l),%WORK(l) 

%WORK(l) ,PSW.NTM 

ISPC%SYSINDX 

%DN (1) , 2 

%WORK(l) ,DCB.ISP(%DCB(1)) 



FETCH CURRENT PSW 

CPU OR IOP? 

CPU -> 

FULLWORD INDEX 

ISP ADDRESS FOR THIS 

PROCESSOR 

%ITEM(1) ,0(%WORK(l) ,%DN(1)) STUFF ENTRY 

%DN(1),2 RESTORE 

ISPX%SYSINDX EXIT 
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ISPC%SYSINDX EQU 
SLLS 

L 

STH 
SRLS 
ISPX%SYSINDX EQU 
MEND 



%DN(1),1 

%W0RK(1) ,DCB.ISP(%DCB(1)) 

%ITEM (1) , O (%WORK (1) , DN (1) ) 
%DN(1),1 



HALFWORD INDEX 

ISP ADDRESS FOR THIS 

PROCESSOR 

STUFF ENTRY 

RESTORE 



ADDSQ 



%LABEL ADDSQ 


%I TEM= , %DCB= , %WORK= 


%LABEL LABEL 




L 


%WORK (1) , DCB . SQ (%DCE 


BNZ 


ADDI%SYSINDX 


LA 


%WORK(l) , SQ 


ADDI%SYSINDX EQU * 




ATL 


%ITEM(l),0(%WORK(l)) 


EPSR 


%WORK(l),%WORK(l) 


TI 


%WORK(l) ,PSW.NTM 


BZ 


ADD%SYSINDX 


LIS 


%WORK(l) ,4 


PINT 


%WORK(l) 


ADD%SYSINDX EQU * 




MEND 





SQ OR SIQ ADDRESS 
NON-ITAM DEVICE 
FOR ITAM DEVICES 

STUFF THE ITEM 
CURRENT PSW 
CPU OR I OP? 
CPU -> 
LEVEL 4 . . . 
. . .KICKOFF 
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APPENDIX D 



OS/32 SUBROUTINE DEFINITIONS 



SERVICE ROUTINES 



NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTER USED: 

ON ENTRY 

ON EXIT: 



IODGST 

This routine returns the status to the SVC1 parameter 
block. 

IODGST, IODGST2 

DCB, IOB, SVC1 

III, ISPTAB 

R4, R6, RC, RE, RF 

R4 = Return address 
R6 = A (DCB) 

RC, RE, RF destroyed 

RF contains status codes 

CC is negative if bad status returned 



PRINCIPLES OF OPERATION: 

At entry, RC is loaded with the address of the parameter block and the interrupt service pointer 
table (ISPT) reset flag is tested. If it is not reset, it is done by loading RF with address of III and 
setting it at the entry for this request in ISPT. The FC is loaded from the DCB and tested for a 
command request. If not command request, move transfer length (LLXF) from device control 
block (DCB) to parameter block, which is skipped for command. Next the STAT field is 
transferred from DCB to PB and a BZR R4 is executed if this field is zero. If nonzero, the 'L' flag 
of CC is set and exit is performed via R4. 

The alternate entry IOPGST2 is the same as IODGST except that the testing and resetting ISPTAB 
code is skipped. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTERNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



IODTWT 

This routine tests for TRAP and WAIT bits and 
performs the requested function. 

IODTWT, IODTWT2 

IOB, TSW 

TMREMW, SV9.ATQ1 

R4, R5, R8-RA, RD, RF 

R4 = Retrun address 
R5 = A (IOB) 

R8-RF may be destroyed 



PRINCIPLES OF OPERATION: 

At entry, R9 is loaded with the address of the task control block (TCB) and the input/output block 
(IOB) request dependent flag field (IOB.RFLG) is tested to see if caller expects an input/output 
(I/O) TRAP. If so, the reason code of the task's trap queue is set to X'08'; a BAL to SV9.ATQ1 is 
performed to make the queue entry with the unrelocated parameter block address in register RA. If 
no trap is expected, this operation is skipped, in which case both paths lead to the checking of the 
flag field of IOB again, this time for the I/O WAIT bit. If this bit is reset, then return via R4. If 
I/O WAIT is indicated, RD is loaded with Y'8000' and a BAL to TMREMW is performed; upon 
return from the task manager, an exit via R4 is performed. 

Entry at the alternate entry IODTWT2 loads R9 with the TCB address and then checks for I/O 
WAIT as in the above. I/O Traps are not tested when entered at this label. 
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UTILITY ROUTINES 



NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



EVMOD 

This routine modifies the event service routine (ESR) 
address to an address specified in register RE. 

EVMOD 

EVN, DCB structures 

NONE 

R8, R9, RE, RF 

R8 = LINK 
RE = A (ESR) 
RF = A (leaf) 

SAME AS ENTRY 
R9 will be destroyed 



PRINCIPLES OF OPERATION: 

Upon entry, R9 is loaded with the address of the DCB from the leaf. If R9 is zero, the leaf is not 
connected; therefore, return via R8. If R9 is nonzero, the address of ESR specified in RE has its 
most significant bit set (bit 0) to indicate modification by EVMOD. The ESR address is stored at 
DCB.ESR. Return to caller via R8. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



EVREL 

This routine disconnects a DCB from the tree beginning 
at the requested level via a call to COMDIS. 

EVREL, NSEVREL 

EVN 

COMDIS 

R6-R9 

R8 = LINK 

RE = REQUEST LEVEL 

RF = leaf ADDRESS 

ALL REGISTERS PRESERVED 



PRINCIPLES OF OPERATION: 

The two entries, EVREL and NSEVREL are equivalent. At entry, registers R4-RF are saved and 
RF is copied to R7, while RE is copied to R9, followed by the loading of R6 with the address of the 
DCB obtained from the leaf. A BAL to COMDIS is executed to do the disconnect and when 
returned, registers R4-RF are restored and return to caller via R8. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



GETIOB 

This routine allocates an IOB from the free list 
maintained by each TCB. 

GETIOB 

TCB, IOB 

NONE 

R8, RA, RB 

ES STATE 
R8 = LINK 
R9 = A (TCB) 

ES STATE 

RA = A (IOB) 

RB = DESTROYED 



PRINCIPLES OF OPERATION: 

Upon entry, RA is loaded from the top of the IOB list specified in the TCB. If the list is empty and 
safety checks are sysgened in, a system crash ensues with a Crash Code 220*. If list is not empty, 
the IOB list pointer is reestablished in the TCB with the address of the next IOB. In the current 
IOB, the forward pointer is zeroed, as is the FC, LU, and STAT entries, as well as the parameter 
block address, flags, and the IOB DONE executor address. The buffer start address and random 
record pointer are set to -1. A return to the caller through R8 is performed. 

"This condition should not exist. If a previous I/O and proceed used the last IOB, the task should 
have been placed in connection wait at that time. See the SVC1EXIT subroutine definition. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



RELIOB 

This routine releases an IOB and returns it to the free 
list of the TCB. 

RELIOB 

IOB, TCB 

NONE 

R8, RA, RB 

ES State 
R8 = LINK 
R9 = A (TCB) 
RA = A (IOB) 

RB DESTROYED 

ALL OTHERS PRESERVED 



PRINCIPLES OF OPERATION: 

Upon entry, the IOB is tested for type validity (TCB as opposed to spare TCB), and if invalid (not 
TCB), a crash with Crash Code 221 is performed if safety checks are sysgened in. For a valid IOB, 
the top of list pointer from the TCB (TCB.IOBL) is loaded and stored in the current IOB forward 
pointer. The address of the current IOB is then stored in the top of list pointer and an exit to caller 
is performed. 
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SQSMLV (Multilevel Device Driver Scheduler) 

SQSMLV dispatches the service routine for devices not 
on a single level. Coordination with upper modes is 
performed prior to dispatch. 

SQS.MLV 

DCB, IOB, EVN 

None 

E8 - EB, ED, EF 

In Es State 
ED = A (DCB) 
EF = A (leaf) 



NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 

PRINCIPLES OF OPERATION: 

Upon entry, the DCB dependent request flags are checked to ensure an EDMA connection or 
connection complete, and if so, the service routine is dispatched. If not, RB is loaded from the upper 
node pointer in the leaf. If RB is zero, dispatch the service routine. If not zero, the leaf flag is 
checked for the EDMA node and the level is checked for availability. If not available, go to 
SQSMSTOP and queue DCB to this node; if so, connect DCB to this node, bump level and retry for 
EDMA node. If the EDMA node is found, BAL to EDMAQCON to either connect to the node or 
queue the DCB for this node. When returning from EDMAQCON, if the node is gotten, dispatch 
the service routine. If queued, exit to SQS.EX. 
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EXIT ROUTINES 



NAME: 


DIRDONE 


ABSTRACT: 


DIRDONE is 




Driver Initiali; 


ENTRYS: 


DIRDONE 


SOURCE LIBRARY ROUTINES: 


DCB 


EXTRNS: 


SQ 


REGISTERS USED: 


ED-EE 


ON ENTRY: 


ES STATE 


ON EXIT: 


UD = A (SQ) 




ES STATE 



DIRDONE is a common exit routine for standard device 



PRINCIPLES OF OPERATION: 

Upon entry, ED is loaded from SQS.DCB save area. Register EE is loaded from the DCB.ESR 
field of the DCB. If the most significant bit is set, this area has already been set by EVMOD and 
hence an exit to system queue service (SQS) is performed. If not set be EVMOD, the "ESR" 
(termination phase of the driver) address is fetched from the DCB and saved at the dispatch pointer 
in the DCB (DCB.ESR). Thereafter, ED is loaded with the address of the SQ and exit is made to 
SQS to check for entries on SQ. 
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NAME: 


EVRTE 


ABSTRACT: 


This routine is 




driver Event J 


ENTRYS: 


EVRTE 


SOURCE LIBRARY ROUTINES: 


NONE 


EXTRNS: 


SQ 


REGISTERS USED: 


UD 


ON ENTRY: 


ES STATE 


ON EXIT: 


ES STATE 




ED = A (SQ) 



This routine is the common exit path for standard device 



PRINCIPLES OF OPERATION: 

Upon entry, ED is loaded with the address of the SQ and an unconditional branch is made to SQS. 
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NAME: 
ABSTRACT: 



ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



IODONE 

This routine is the normal or error termination from 
standard device driver ESR's. It returns status to users' 
SVC1 PBLK, sets requested task trap, removes I/O 
WAIT, and disconnects leaf. 

IODONE, IODONE2 (Same as IODONE) 

DCB, IOB 

NONE 

R3 - R8, RD, RF 

ES STATE 
RD = A (DCB) 
RF = A (leaf) 

ES STATE 

RD = A (SQ) 

RF = A (PARAM BLOCK) 



PRINCIPLES OF OPERATION: 

Upon entry, the ABORT I/O flag is reset and the address of a special IODONE executor is loaded. 
If address nonzero, branch to this routine. If zero, R3 is loaded with the request dependent flags, 
arid with the leaf address in RF and load RS with the IOB address, BAL to IODTWT to check 
TRAP and I/O WAIT conditions. When returned, the parameter block address is loaded to check 
for console dummy driver. If not, set status to parameter block and test for disconnect required 
(ITAM). If nonrequired, exit to SQS and check system queue. If ITAM device, load leaf address, 
set level counter, and BAL to COMDIS to disconnect from leaf and tree. Upon return, exit to SQS. 
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QUEUEING ROUTINES 



NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



COMDIS 

This routine disconnects a DCB from the tree starting 
from the requested level. 

COMDIS 

DCB, IOB, EVN, TCB 

TMREMW 

R4-RF 

R4 = LINK 
R6 = A (DCB) 
R7 = A (leaf) 
R9 = Request level 

R8 - RF may be destroyed 



PRINCIPLES OF OPERATION: 

Upon entry, the DCB and leaf addresses are copied to RD and RB, respectively, and the Connection 
Complete and Seek Check flags are reset in the DCB. Next the level is checked to see if it is the 
leaf level (=1) to start with first. If it is not a leaf, a loop is entered to go up levels until the 
appropriate level is found; it is tested for direct memory access (DMA) level and if so a BAL to 
EDMADIS is performed. If not DMA, a BAL to node DIS is executed. When returned, if more 
must be released, the EVN. CORD pointers are followed to next item until we have released all 
upper nodes to the EDMA node. At this point, return to caller is via R4. 

If level to be released is a leaf, then the address of the IOB is fetched from the DCB and the IOB 
flags are tested for system buffered I/O. If the I/O count of the TCB is decremented by 1 and in 
either case the DCB is now disconnected from the leaf by setting EVN .DCB to zero, the queue is 
interrogated to see if it is empty, and if so the top and bottom pointers are set to zero. If not, the 
top pointer is adjusted and a BAL to LEAFCON is performed to connect top DCB in queue to leaf. 
Upon return, the leaf address is added to the SQ. The IOB flags are checked to see if it can be 
released now or not. If so, the IOB is released, the TCB is checked for any wait states, and we then 
proceed up the tree to next mode and process as in the above for either a node or EDMA node. 
Return to caller is via R4. 
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NAME: 
ABSTRACT: 



ON EXIT: 



COMFIFO 

The routine adds an IOB to the bottom of a leaf 
QUEUE or a leaf/node to the bottom of a node 
QUEUE. 



ENTRYS: 


COMFIFO 


SOURCE LIBRARY ROUTINES: 


NONE 


EXTRNS: 


NONE 


REGISTERS USED: 


R8 -RB 


ON ENTRY: 


R8 = LINK 



R9 = LEVEL NUMBER 
RA = A (IOB/leaf/node) 
RB = OWNER OF QUEUE 

RC is destroyed 
CC is negative 



PRINCIPLES OF OPERATION: 

Upon entry, the level number is checked to see if it is greater than total number of nodes, and if so, 
a system crash with Crash Code 203 results. A crash also occurs if the level number is either 
negative or zero. If the leaf level is for a leaf, (level = 1) exit to LFIFO and queue the IOB. If 
level is not for leaf, exit to NFIFO to queue the leaf or node. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



COMQ 

This routine is a common queue routine which branches 
to appropriate queue handler depending upon the level 
number. 

COMQ 

NONE 

NONE 

E8 -EB 

EA = A (IOB/leaf/node) 
EB = OWNER OF QUEUE 
E8 = LINK 
E9 = LEVEL NUMBER 

EA & EB passed to QUEUE ROUTINES 



PRINCIPLES OF OPERATION: 

When entered, the level number in E9 is compared to see if it is greater than the total number of 
nodes, and if so, a system crash with Crash Code 203 results. Otherwise, the contents of E9 are 
aligned to a fullword boundary. If the level number is zero, a system crash of 203 also results. If 
nonzero, the queue routine address is loaded from the CQTABLE and unconditionally branched to 
for execution. 
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NAME: 

ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



DISKNODE 

This routine queues a leaf or node to an upper node. 

NONE 

NONE 

NONE 

R8 - RF 

R8 = LINK 

R9 = LEVEL NUMBER 

RA = A (IOB/leaf/node) 

RB = owner of queue (leaf/node) 

RD = A (DCB) 

Nothing modified 



PRINCIPLES OF OPERATION: 

Upon entry, the level is checked for the disk controller level (=2) and if so, a branch to NFIFO to 
do a first-in/first-out (FIFO) queue is executed. If not, BAL to SEEKCHK to decide if a seek is 
necessary. If so, branch to NLIFO to set last-in/first-out (LIFO) queuing. If seek not necessary, 
branch to NFIFO. 
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NAME: 
ABSTRACT: 



ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



DISKQ 

This routine handles the queuing of IOB's and nodes for 
disk I/O. Branching to appropriate queue routine is 
performed depending upon the level number of the 
request. 

DISKQ 

IOB, DCB, EVN 

NONE 

R8-RF 

R8 = LINK 

R9 = LEVEL NUMBER 

RA = A (IOB/leaf/node) 

RB = owner of QUEUE (leaf/node) 

RD = A (DCB) 

RC RE, RF destroyed 
CC is negative 



PRINCIPLES OF OPERATION: 

Upon entry, the level number is compared against the maximum and, if found to be greater, a 
system crash with Crash Code 203 results. If the level is the EDMA level (=4), then a branch to 
NFIFO is executed to queue on FIFO basis. If it is an intermediate level, then go to DISKNODE to 
queue the leaf or node to upper node. If level is leaf (=1), the waiting queue is interrogated. If 
empty, then the contents of RA is queued to the bottom of this queue, and if this is for active TCB, 
then it is queued to the 'top,' as well as to 'wrap.' An exit is then performed through R8 after 
setting the 'L' flag of CC. If the top of queue equals the wrap, then the item is placed at the top, 
the IOB is inserted into queue, and exit. If it is the same, then it is placed on the secondary queue, 
and exit. If the top of the queue is not equal to wrap, then the random address from the IOB is 
loaded and compared to the current sector pointer. If we are beyond the current sector, then this 
request is wrapped. If it is less than the current sector, then put this request into the IOB request 
queue in proper order. If this is the current active TCB request, then put onto secondary queue and 
exit. If not current TCB, set it on the top of the queue, insert the IOB, and exit. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



EDMACON 

This routine either connects a node to EDMA or rejects 
the request. 

NONE 

EVN, DCB, IOB 

NONE 

R9 - RF 

R9 = LINK 

RA = A (node) 

RB = A (EDMA node) 

RD = A (DCB) 

RC, RE, RF are destroyed 
CC is clear if connection made 
CC is negative if no connection 



PRINCIPLES OF OPERATION: 

Upon entry, the EDMA node is checked to see if it is already connected, and if so, the CC is set to 
negative and return to caller via R9 is performed. Next the request is made for an 'Exclusive' 
connection and if so, the EDMA transfer counter (EVN; ECTR) is checked for activity. If zero, the 
'Exclusive' request active flag is set and connection is made by incrementing the EDMA transfer 
counter by one, setting the connect flag in the DCB, clearing the CC, and returning via R9 to the 
caller. 

If the EDMA 'Exclusive' transfer flag is reset, the EDMA transfer counter is compared with the 
EDMA 'Maximum' and if found equal, this request is rejected as above with CC set negative. If 
not equal, then normal connection is accomplished as above. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



EDMADIS 

This routine disconnects a DCB from an EDMA node, if 
connected, and connects as many queued nodes as 
possible. 

NONE 

DCB, IOB, EVN 

SQ 

R8 - RB, RD RF 

R8 = LINK 

RB = A (EDMA node) 

RD =3 A (DCB) 

R9, RA, RC, RE, RF may be destroyed 
CC is negative if DCB not connected 
CC is clear if DCB was connected 



PRINCIPLES OF OPERATION: 

Upon entry, the DCB request dependent flags are examined to determine if the DCB is connected to 
the EDMA node. If not, the CC is set to negative and a return to caller via R8 is performed. If 
connected, then the connect flag and exclusive active flag of the DCB and node, respectively, are 
cleared and the EDMA ACTIVE Counter of the node is decremented by one. If the node top of 
queue is zero (queue empty), then a normal exit is performed with CC cleared. If queue is not 
empty, then it is checked to see if it is the last item. If so, it is removed and 'top' and 'bottom' 
pointers are set to zero. A BAL to EDMACON is performed in attempt to queue this item. If item 
is queued, the leaf of new DCB is added to the SQ and a return to check for another queue item is 
made as above. If the connection was not made, the item is added to the EDMA queue, the 
forward pointer is set, CC is cleared, and return to caller via R8 is performed. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



EDMAQCON 

If EDMA is needed, this routine either queues or 
connects a node to the EDMA level. 

EDMAQCON 

DCB, IOB 

NONE 

R8-R9, RA-RB, RD, RF 

R8 = LINK 

RA = A (LOWER node) 
RB = A (EDMA node) 
RD = A (DCB) 

R9, RC, RE, RF may be destroyed 

CC clear if connected or EDMA not required 

CC negative if node is queued 



PRINCIPLES OF OPERATION: 

Upon entry, the DCB is examined to inspect the EDMA strategy routine address, and if found to be 
zero, a BAL to EDMACON is performed in attempt to connect the leaf. A successful connection 
results in return to caller via R8. Unsuccessful connection causes an unconditional branch to the 
queuing strategy routine pointed to by the DCB with R9 loaded with 4 in order to set the level. If 
the EDMA strategy routine address is nonzero, a BAL to this routine is performed to determine if 
EDMA is needed, and if so, an attempt is made to connect as above. If not needed, the Connection 
Complete Flag in the DCB is set, the CC is reset, and a return to caller via R8 is performed. 



D-18 



48-190 F00 R00 



NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



LEAFCON 

This routine connects an IOB to a leaf. All IOB 
information^ moved to the DCB. 

LEAFCON 

IOB, DCB 

NONE 

E9, EC, EF 

R8 = LINK 
RA = A (IOB) 
RB = A (leaf) 

RA = A (DCB.IOB) 

RB = A (leaf) 

RC = A (CONNECT DCB) 

R9 = A (CONNECT TCB) 

RD & RE Preserved others may be destroyed 



PRINCIPLES OF OPERATION: 

Upon entry, the DCB address is loaded from IOB and stored into the EVN (leaf). The IOB 
information is then moved to the DCB. These items are: request dependent flags, IODONE 
processor address, the address of the TCB, the addresses of the driver initialization routine, start 
and end, unrelocated parameter block, relocated parameter block, the FC, lu, and STAT fields, 
random number, and lu entry. Exit is via R8. 
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NAME: 

ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



LEAFQ 

This routine queues an IOB to a leaf. 

LEAFQ 

EVN, DCB 

NONE 

R8 -RC 

R8 = LINK 
RA = A (IOB) 
RB = A (leaf) 

RA, RB Preserved 
others may be destroyed 



PRINCIPLES OF OPERATION: 

Upon entry, R9 is set to contain level number 1, the DCB queue routine is loaded into RC, and if 
zero, a branch to COMQ is performed. If queue routine is defined, branch to this routine via RC. 
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NAME: 

ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



LFIFO 

This routine adds an IOB to the bottom of a leaf queue. 

LFIFO 

IOB, EVN 

NONE 

R8-RC 

R8 = A (RETURN) 

RA = A (IOB) 

RB = owner of leaf queue 

RC is destroyed 
CC is negative 



PRINCIPLES OF OPERATION: 

Upon entry, the forward pointer of the IOB is cleared and the bottom of the leaf queue is loaded. If 
zero (queue empty), then the IOB is set to the top and bottom of the queue, the CC 'L' flag is set, 
and exit is via R8. If the bottom of queue is not zero, the IOB is set to be the forward pointer of 
current bottom and the IOB becomes the new bottom, thereby setting the 'L' flag of CC and exiting 
via R8. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



NFIFO 

This routine adds an item to the bottom of a node (leaf) 
queue. 

NFIFO 

EVN 

NONE 

R8 -RC 

R8 = LINK 
RA = A (ITEM) 
RB = owner of queue 

RC is destroyed 
CC is negative 



PRINCIPLES OF OPERATION: 

Upon entry, the forward pointer of the node (leaf) is cleared in the item to be queued. The node 
(leaf) bottom of the queue is loaded and if zero, a new entry is being made, in which case the item 
address is set at the queue top pointer as well as the bottom. If it is nonzero, then the item to be 
added becomes new bottom with its address set at the forward pointer in the previous bottom to 
maintain the list. The 'L' flag of CC is set and an exit via E8 is performed. 
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NAME: 

ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



NLIFO 

This routine places an item on the top of a node's queue. 

NLIFO 

EVN 

NONE 

R8, RA - RB, RF 

R8 = LINK 
RA = A (ITEM) 
RB = owner of queue 

RF is destroyed 
CC is negative 



PRINCIPLES OF OPERATION: 

Upon entry, the top pointer of the node's queue is loaded and if queue is empty, the item is added 
to bottom pointer of queue. If not empty, the item in RA is placed at the top of the queue. The 
address of the previous top is stored at the item's forward pointer. The 'L' flag of the CC is set and 
an exit is performed via EA to caller. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 



ON EXIT: 



NODECON 

This routine connects a lower node (leaf) to an upper 
node. 

NONE 

EVN 

NONE 

R8, RA ■ RD, RF 

R8 = LINK 

RA = A (LOWER node or leaf) 

RB = A (UPPER node) 

RD = A (DCB) 

RC is destroyed 



PRINCIPLES OF OPERATION: 

Upon entry, the DCB address is set into the upper node flagging it as being used, the CC is reset, 
and an exit via R8 is performed. 
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NAME: 


NODEDIS 


ABSTRACT: 


This routine d 




connects the top 


ENTRYS: 


NONE 


SOURCE LIBRARY ROUTINES: 


EVN, DCB 


EXTRNS: 


SQ 


REGISTERS USED: 


R8 - RD, RF 


ON ENTRY: 


R8 = LINK 




RB = A (node) 




RD = A (DCB) 



ON EXIT: 



RA, RC, RD may be destroyed 

CC is negative if node was not connected 



PRINCIPLES OF OPERATION: 

Upon entry, the contents of RD is compared with EVN.DCB to see if the node is connected. If not, 
the 'L' flag is set in the CC and an exit via R8 is executed. If connected the node DCB field is 
cleared and the queue top pointer is examined. If empty, return via R8; if not empty, check the 
queue bottom to see if it is the last item. If it is, zero bottom pointer; if not, fetch the next item and 
reset the top pointer to this item (or if last item). Fetch the DCB address and leaf address from 
previous top of queue and add leaf address to top of the SQ list. Fall through to routine 
NODECON and exit. 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISERS USED: 

ON ENTRY: 



ON EXIT: 



NODEQCON 

This routine either connects a node or leaf or will queue 
a node or leaf if it is unavailable. 

NONE 

EVN, DCB 

NONE 

R8 - RD 

R8 = LINK 
R9 = connect level 
RA = lower node (leaf) 
RB = upper node (leaf) 
RD = A (DCB) 

RC destroyed 

if queued, R9 - RF may be destroyed 



PRINCIPLES OF OPERATION: 

At entry, RC is loaded with the DCB address from the node (leaf). If zero, branch to NODECON 
to connect this DCB to node (leaf). If non-zero, this node (leaf) is unavailable and request must be 
queued. The queue strategy is loaded from the DCB and if nonzero, exit to this routine. If zero, 
fall into routine NFIFO. 
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PRTYQ 

This routine performs the priority queue handling by 
ordering the wait queue by priority. 

PRTYQ 

EVN, IOB 

NONE 

E8-ED 

EA = A (IOB) 
EB = A (leaf/node) 
E8 = LINK 



NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 

PRINCIPLES OF OPERATION: 

Upon entry, the top of the node's (leaf's) wait queue is loaded. If empty, the IOB address goes on 
the top and bottom of the list, the IOB forward pointer is reset, the CC has the 'L' flag set and 
return is by way of E8. If nonempty, the priority of the IOB to be inserted is compared with the 
priority of the queued top. If 'new' is less than or equal to 'bottom,' append 'new' at the bottom. If 
in between, then the queue is searched by priority and the new IOB is inserted in the appropriate 
place. In all cases, exit is made via E8 after the 'L' flag is set in the CC (Condition Code). 
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NAME: 
ABSTRACT: 

ENTRYS: 

SOURCE LIBRARY ROUTINES: 

EXTRNS: 

REGISTERS USED: 

ON ENTRY: 

ON EXIT: 



SEEKCHK 

This routine decides whether a seek is necessary, flags 
the DCB with the result, and notifies the caller. 

SEEKCHK 

DCB, IOB 

NONE 

R9, RC - RF 

R9 = LINK 
RD = A (DCB) 

R8 - RB, RD Preserved 

RC, RE, RF, destroyed 

CC is zero if seek necessary 

CC is negative if no seek necessary 



PRINCIPLES OF OPERATION: 

Upon entry, the DCB request flags are checked to see if a seek check had already been performed, 
and if not then one is executed. If it had, the IOB 'seek necessary' flag is checked to see if a seek 
must be performed. If not, the CC 'U flag is set and exit is via R9. If yes, then set the CC to zero 
and exit via R9. If a seek check must be performed, the number of tracks per cylinder is loaded 
from the DCB and the number of sectors per cylinder is computed; the DCB.RAND pointer is 
loaded and diminished by DCB.CSEC. If the current sector is the same as random, then no seek is 
needed and the flags are set in the DCB to indicate such, CC 'L' flag is set, and exit is made via 
R9. If not current sector, a check is made to see if it is the same cylinder, and if so, the DCB flags 
are set, CC is set to zero, and the exit is via R9. If not the same cylinder, then a seek must be 
performed; therefore, set flags in DCB and return to caller with CC set to zero. 
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APPENDIX E 



SKELETON DRIVER AND ASSOCIATED DCBXXX MACRO 



INITSKEL 

This module is the body of the skeleton driver. It includes the structure definitions (from the 
standard system libraries), the initialization, interrupt service and termination routines. 



NOTE 

This driver performs all necessary functions (e.g., setup of 
the interrupt service table, call to TOCHON, etc.) explicitly 
for purposes of illustration. Standard subroutines are 
supplied in the file SUBS.MAC (INITSUBS in the standard 
DRIVER.LIB), which perform many of these functions. 



MLIBS 8,9,10 
INITSKEL PROG PERKIN-ELMER OS/32 SKELETON DRIVER 



TITLE STRUCTURE AND MNEMONIC DEFINITIONS: 
* INCLUDE STANDARD SYSTEM STRUCTURES: 
$PDCB 
$CCB 
$REGS$ 



* DEFINE 


DEVICE -DEPENDENT DCB 




STRUC 






DS 


DCB . DVDP 


DCB . CCB 


DS 


2 


DCB . XDCD 

* 


DS 


2 


DCB . XXXX 
* 


DSF 
ENDS 


1 



DEVICE -INDEPENDENT PORTION 
A (CCB) 

EXT'D DEV CODE FROM SYSGEN INPUT 
(SEE DCB MODULE) 
OTHER DEVICE -DEPENDENT FIELDS 
DEFINED HERE. 
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* MNEMONIC DEFINITIONS: 
TOUTSKEL EQU 5 



5 SECOND TIMEOUT (FOR EXAMPLE) 



* EXTERNAL REFERENCES: 
EXTRN ISPTAB 
EXTRN TOCHON 
EXTRN TOCHOFF 
EXTRN SQ 
EXTRN DIRDONE 
EXTRN IODONE2 
EXTRN IODONE 



INTERRUPT SERVICE TABLE 

PUT DCB ON TIMER CHAIN 

TAKE DCB OFF TIMER CHAIN 

SYSTEM QUEUE 

EXIT FROM DRIVER INITIALIZATION 

ERROR EXIT FROM DVR INIT 

FINAL EXIT FROM DRIVER 



TITLE DRIVER INITIALIZATION ROUTINE 

IMPUR 

ENTRY INITSKEL,TERMSKEL 



INITSKEL EQU 



* ENTER HERE FROM SYSTEM QUEUE SERVICE. 

* BY SVC 1 SUPERVISOR. 



INIT ROUTINE IS SCHEDULED 



* UPON ENTRY: 
* 



UD = ADDRESS OF DCB 

UF = ADDRESS OF LEAF 

DCB.FC(UD) = SVC 1 FUNCTION CODE 

DCB.SADR(UD) = SVC 1 BUFFER START ADDRESS (RELOCATED) 

DCB.EADR(UD) = SVC 1 BUFFER END ADDRESS (RELOCATED) 

DCB. RAND (UD) = SVC 1 RANDOM ADDRESS FIELD 

DCB.PBLK(UD) = SVC 1 PARAMETER BLOCK ADDRESS (RELOCATED) 



* INSERT ANY DEVICE DEPENDENT INITIALIZATION HERE... 

* INCLUDING BUFFER ALIGNMENT CHECKS, FUNCTION CODE CHECKS, ETC. 

* ON ERROR, SET DCB. STAT AND DCB.DDPS TO DESIRED ERROR CODE AND 

* EXIT VIA IODONE2. 
* 

* OTHERWISE, START UP THE DEVICE AS FOLLOWS: 



* SET UP ISPTAB WITH CCB ADDRESS + 
LHL U4,DCB.DN(UD) 
LHL UC , DCB . CCB (UD) 
LA UB,1(UC) 



GET DEVICE NUMBER 
GET CCB ADDRESS 
UB := A(CCB)+1 
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STH UB,ISPTAB(U4,U4) SET ODD CCB ADDR IN ISPTAB 

* SET UP CCB FOR NO-EXECUTE: 

LI UO,CCWSTAT 
STH UO,CCB.CCW(UC) 

* SET UP 1ST ISR ADDRESS IN CCB: 

LA UO,ISROSKEL 
STH UO,CCB.SUBA(UC) 

* NOW PUT DCB ON TIME-OUT CHAIN: 

BAL U8 , TOCHON 

* SIMULATE INTERRUPT ON DEVICE TO GET INTO 1ST ISR. 

* THIS IS ANALOGOUS TO A SUBROUTINE CALL ON THE 1ST ISR. 

* ALL I/O IS NORMALLY DONE IN THE ISR. 

LHL U8,DCB.ILVL(UD) GET SYSGEN'D INTERRUPT LEVEL 
SINT U8,0(U4) "CALL" THE ISR 

* NORMAL INIT ROUTINE EXIT IS TO DIRDONE : 

B DIRDONE 



TITLE INTERRUPT SERVICE ROUTINES 
PURE 

* NOTE THAT THE ISRS ARE CODED AS "PURE". LINK PROCESSES THIS PURE 

* CODE TO ABSOLUTELY INSURE THAT THE ISRS ARE IN THE 1ST 64KB OF 

* MEMORY. THIS IS REQUIRED BY THE P-E 3200 SERIES ARCHITECTURE BECAUSE 

* THE INTERRUPT SERVICE TABLE CONTAINS HALFWORD (16-BIT) POINTERS. 
* 

* NOTE ALSO THAT THE EXECUTIVE REGISTER MNEMONICS ARE USED TO 

* REMIND US THAT WE ARE IN THE EXECUTIVE REGISTER SET ASSOCIATED 

* WITH THIS INTERRUPT LEVEL. 
* 

* ! ! ! ! BY CONVENTION, ONLY REGISTERS EO THRU E7 MAY BE USED ! ! ! ! 
ISROSKEL EQU * 

* ENTER HERE FROM SIMULATED INTERRUPT IN THE DIR. 
* 

* ON ENTRY: (SET UP BY MICROCODE) 

* 

* EO = OLD PSW STATUS (IN DIR) 
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El = OLD LOG COUNTER (RETURN TO DIR) 

E2 = INTERRUPTING DEVICE NUMBER 

E3 = DEVICE STATUS 

E4 = A(CCB) - GET A(DCB) FROM CCB.DCB(E4) 

ANY DEVICE INITIALIZATION IS NORMALLY PERFORMED HERE, 

INCLUDING STATUS CHECKS, OUTPUT COMMANDS, ETC. 

THEN DEVICE TIMEOUTS ARE ENABLED, CCB.SUBA IS SET UP TO INTERCEPT 

THE NEXT INTERRUPT AND WE RETURN TO THE DIR. 



GET DCB ADDRESS 

TIMEOUT CONSTANT (IN SECONDS) 

START TIMER 



L 


E5, 


CCB. DCB (E4) 


LI 


E6, 


. TOUTSKEL 


STH 


E6, 


, DCB. TOUT (E 5) 


LA 


E6. 


ISR1SKEL 


STH 


E6, 


CCB.SUBA(E4) 


LPSWR 


EO 





NEXT ISR ADDRESS 
SET IN CCB 

RETURN TO DIR BY LOADING OLD PSW 



ISR1SKEL EQU * 

* ENTER HERE WHEN THE DEVICE GENERATES AN INTERRUPT. 
* 

* ON ENTRY: (SET UP BY MICROCODE) 
* 

OLD PSW STATUS (IN INTERRUPTED CODE) 

OLD LOC COUNTER (IN INTERRUPTED CODE) 

INTERRUPTING DEVICE NUMBER 

DEVICE STATUS 

A (CCB) - GET A (DCB) FROM CCB. DCB (E4) 

* BY CONVENTION THE 1ST THING WE MUST DO IS TEST THE TIMEOUT 

* CONSTANT IN THE DCB. IF IT IS ZERO, THIS INTERRUPT IS TOO LATE. 

* THE OS HAS ALREADY SCHEDULED DEVICE TERMINATION. 



* 


EO = 


* 


El = 


* 


E2 = 


* 


E3 = 


* 


E4 = 


* 





L E5,CCB.DCB(E4) 
LH E6, DCB. TOUT (E6) 
BNP ISRTOUT 



GET DCB ADDRESS 
TEST TIMEOUT VALUE 
TOO LATE, GET OUT ! 



! ! 
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* ANY DEVICE DEPENDENT CODE WOULD BE INSERTED HERE. 

* SUCH AS STATUS CHECKS, DATA TRANSFER, OUTPUT COMMANDS. 

* 

* IF ANY ERRORS ARE ENCOUNTERED WHICH REQUIRE IMMEDIATE TERMINATION, 

* LOAD E7 WITH A STATUS CODE (E.G., X'8400') AND EXIT VIA ISR.STAT 

* BELOW WHICH SCHEDULES DRIVER TERMINATION. OTHERWISE... 

* 

* THIS ISR MIGHT HANDLE MULTIPLE DEVICE INTERRUPTS. 

* AT SOME POINT, WE WILL SET UP CCB.SUBA TO POINT TO THE FINAL 

* ISR: 

LA E6,ISRNSKEL FINAL ISR ADDRESS 

STH E6, CCB.SUBA (E4) SET IN CCB 

LPSWR EO RESUME INTERRUPTED CODE 



ISRNSKEL EQU * 

* ENTER HERE ON FINAL INTERRUPT FROM THE DEVICE. 
ON ENTRY: (SET UP BY MICROCODE) 



* 



* EO = OLD PSW STATUS (IN INTERRUPTED CODE) 

* El = OLD LOC COUNTER (IN INTERRUPTED CODE) 

* E2 = INTERRUPTING DEVICE NUMBER 

* E3 = DEVICE STATUS 

* E4 = A (CCB) - GET A(DCB) FROM CCB.DCB(E4) 
* 

* AGAIN, WE MUST 1ST CHECK THAT THE DRIVER HAS NOT BEEN TIMED OUT. 
* 

L E5,CCB.DCB(E4) GET DCB ADDRESS 

LH E6,DCB.T0UT(E5) TEST TIMEOUT VALUE 

BNP ISRTOUT TOO LATE, JUST GET OUT !! 

* DO ANY DEVICE CLEANUP OPERATIONS HERE 

* SET UP DCB. STAT AND DCB.DDPS TO REFLECT STATUS IF DESIRED, OR 

* LEAVE THIS UP TO THE TERMINATION ROUTINE. 
* 

LIS E7,0 SET GOOD STATUS 

ISR.STAT EQU * ERROR EXIT PATH 
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STH E7,DCB.STAT(E5) SET STATUS IN DCB 

* NOW SCHEDULE DRIVER TERMINATION BY ADDING LEAF ADDRESS TO SYSTEM 

* QUEUE. 

* NOTE THAT DCB. TOUT IS SET TO -1 (=X , FFFF*) TO PREVENT THE OS 

* FROM TIMING IT OUT NOW THAT WE HAVE SCHEDULED TERMINATION. 



* 



LCS E7,l GET A -1 

STH E7, DCB. TOUT (E5) ZAP TIMEOUT 

L E7,DCB.LEAF(E5) GET LEAF ADDRESS 

ATL E7,SQ SCHEDULE TERMINATION ESR 

LPSWR EO EXIT FINAL ISR 



ISRTOUT EQU * 

* COME HERE ON ANY INTERRUPT WHICH FINDS DCB. TOUT <= O 

* DO ANY NECESSARY DEVICE DEPENDENT CLEANUP (EG., DISARM) 

* AND/OR JUST EXIT 
* 

LPSWR EO EXIT ISR 



TITLE DRIVER TERMINATION ROUTINE 
IMPUR 
* 

* NOTE THAT THE TERMINATION ESR IS CODED AS IMPUR BECAUSE IT CAN 

* OCCUR ANYWHERE IN MEMORY. I.E., IT IS NOT RESTRICTED TO THE 

* 1ST 64KB. 

TERMSKEL EQU * 

* ENTER HERE FROM SYSTEM QUEUE SERVICE. DRIVER TERMINATION IS 

* SCHEDULED BY THE FINAL ISR OR, IN THE EVENT OF A DEVICE TIMEOUT, 

* BY THE OS ITSELF. WHICH CAN BE DETERMINED BY EXAMINING DCB. TOUT. 
* 

* UPON ENTRY: 
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UD = ADDRESS OF DCB 

UF = ADDRESS OF LEAF 



* BY CONVENTION, 

* ACCORDINGLY. 



WE FIRST TEST EOR TIMEOUT AND SET STATUS 



LH UO, DCB. TOUT (UD) 
BNZ TERM. OK 



DID WE TIMEOUT ?? 
NO, OK 



* DEVICE TIMED OUT... SET APPROPRIATE STATUS: 

LHI U7,X'8282* TIMEOUT STATUS 

STH U7 , DCB . STAT (UD) 

* CLEANUP AS NECESSARY (EG., DISARM THE DEVICE, ...) 

B TERM. END 



TERM .OK EQU * 

* DID NOT TIME OUT. CHECK FOR OTHER POSSIBLE ERRORS, DO ANY 

* NECESSARY CLEANUP, CALCULATE LENGTH OF TRANSFER AND PUT IN 

* DCB.LLXF IF APPROPRIATE... 



TERM. END EQU 


* 


BAL 


U8 , TOCHOFF 


B 


IODONE 


END 





! ! ! REMOVE DCB FROM TIME OUT CHAIN ! ! ! 
FINAL EXIT FROM DRIVER 
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ASSOCIATED DCBxxx MACRO 

The following DCBxx macro definition is provided. Notice how this user has only used the 
necessary macro parameters and deleted the other parameters. 



DEVICE CODE 246 

MACRO 

DCB246 %DCOD=, %DN=, %CLAS= / %ILVL=, %NAME=, %SHCCB=, %COUNT= 
* 

* DEFINE GLOBAL COUNTER FOR DEVICE CODES 
* 

GBLC %IDVAL 

BGBLA %ID246 

* 

LCLC %OFFS 

LCLA %CLASN 

AIF (T'%CLAS EQ *U')&CLSNTD 

%CLASN SETA %CLAS*12 I0CLASS*12 

&CLSNTD ANOP 
* 

USERINIT INITIALIZE STRUC COPY FLAGS 

CONVNUM VAL=%ID246 SET %IDVAL WITH STRING EQUIVALENT 
* 

* CREATE DCB 

DCB_%NAME PROG GENERATE PROGRAM LABEL FOR LINK MAP 

DCBI DC0D=246,SIZE=DCB.DVDP+4, INIT=INITSKEL,TERM=TERMSKEL, 
ATRB=7F00, IOH=COMIOH, ID=%IDVAL, SHCC=1 
* 

* CREATE CCB 
* 

CCBI DC0D=246 , ID=%IDVAL, SUBA=I I I 
* 

CCB%NAME EQU CCB%DC0D%IDVAL 

%ID246 SETA %ID246+1 
* 

* DEFINE SYSTEM DEPENDENT FIELDS OF DCB FIRST 
* 

%OFFS SETC 'SSDCOD' : ^IDVAL 1 ESTABLISH PROPER OFFSET 
ORG DCB%OFFS+DCB.DN DEVICE ADDRESS 
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&NSLEAF 



&NRMLFX 
&NOLEAF 



H'%DN' 

DCB%OFES+DCB.LEAF LEAF POINTER 
(T'%SHCCB' EQ 'U')&NSLEAF 
LF%SHCCB USE SHARED DEVICE LEAF 



GENERATE STANDARD LEAF NAME 



DC 

ORG 

AIF 

DAC 

EXTRN LF%SHCCB 

AGO &NRMLFX 

ANOP 

DAC LF%OFFS 

EXTRN LF%OFFS 

ANOP 

ANOP 



* DEFINE ALTERNATE NAME FOR DMT MACRO 
DCB_%NAME EQU DCB%OFFS 

ENTRY DCB_%NAME 

ORG DCB%OFFS+DCB.DMT 

DC DMT_%NAME A (DMT ENTRY) 

EXTRN DMT_%NAME 



&NOCLAS 



AIF 
ORG 
DC 
ANOP 



(T'%CLAS EQ 'U')&NOCLAS 
DCB%OFFS+DCB.CLAS 10 CLASS 
H*%CLASN' I0CLASS*12 



&NOILVL 

* 

* 



AIF 
ORG 
DC 
ANOP 



(T*%ILVL EQ 'U*)&NOILVL 
DCB%OFFS+DCB.ILVL ILEVEL 
H'%ILVL* 



CONTINUE WITH OTHER DCB OPTIONS 



&NCOUNT 



AIF 
ORG 
DC 
ANOP 



(T'%COUNT EQ 'U'J&NCOUNT 
DCB%OFFS+DCB.DVDP 
%COUNT 



USEREND 
MEND 



MUST END THIS SOURCE MODULE 
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